Ошибка компиляции проекта cuda

1. не #import. Если вы хотите включить cuda.h (в этом нет необходимости), используйте #include. Вместо этого я бы просто удалил эту строку из вашего файла super-resolution.cu.

2. Что вы раньше не показывали, но теперь очевидно, так это то, что в super-resolution.cu вы включаете lodepng.h и также позднее указываете C-связь для двух функций: lodepng_decode32_file и lodepng_encode32_file. Когда я попытался скомпилировать ваш super-resolution.cu, компилятор выдал мне такие ошибки (не знаю, почему вы их не видите):

   super-resolution.cu(8): error: linkage specification is incompatible with previous "lodepng_encode32_file"
   lodepng.h(184): here
   
   super-resolution.cu(9): error: linkage specification is incompatible with previous "lodepng_decode32_file"
   lodepng.h(134): here
   

   Так что в основном вы спотыкаетесь о связи C и C++.

3. Я считаю, что самое простое решение - использовать lodepng.cpp (вместо lodepng.c), удалить следующие строки из вашего super-resolution.cu:

   extern "C" unsigned lodepng_encode32_file(const char* ,const unsigned char* , unsigned , unsigned h);
   extern "C" unsigned lodepng_decode32_file(unsigned char** , unsigned* , unsigned* ,const char* );
   

   И просто скомпилируйте все и слинкуйте все в стиле С++:

   $ g++ -c lodepng.cpp
   $ nvcc -c super-resolution.cu
   nvcc warning : The 'compute_10' and 'sm_10' architectures are deprecated, and may be removed in a future release.
   $ nvcc -o super-resolution super-resolution.o lodepng.o
   nvcc warning : The 'compute_10' and 'sm_10' architectures are deprecated, and may be removed in a future release.
   $
   

4. Если вы действительно хотите связать lodepng.o c-стиль вместо стиля c++, вам нужно будет изменить lodepng.h с соответствующими оболочками extern "C", где вызываются необходимые функции. На мой взгляд, это становится грязным.

5. Если вы хотите избавиться от предупреждений о sm_10, добавьте переключатель nvcc для компиляции для другой архитектуры, например:

   nvcc -arch=sm_20 ...
   

   но убедитесь, что все, что вы выберете, совместимо с вашим графическим процессором.

Вот простой фрагмент кода.

Библиотеку lodepng можно получить отсюда (http://lodev.org/lodepng/).

Если переименовать его в C, его можно будет использовать на C.

Даже на этом уровне возникают проблемы с компиляцией

"undefined reference to `lodepng_decode32_file'"
"undefined reference to `lodepng_encode32_file'"

Файл: Makefile

all:    gpu
    gcc -g -O -c lodepng.c
    nvcc -c super-resolution.cu
    nvcc -o super-resolution-cuda super-resolution.o lodepng.o
    rm -rf super-resolution.o
    rm -rf lodepng.o

Файл: super-resolution.cu

#import "cuda.h"
#include "lodepng.h"

#include <stdio.h>
#include <stdlib.h>
#include <math.h>
#include <cstdio>

extern "C" unsigned lodepng_encode32_file(const char* ,const unsigned char* , unsigned , unsigned h);
extern "C" unsigned lodepng_decode32_file(unsigned char** , unsigned* , unsigned* ,const char* );

//GPU 3x3 Blur.
__global__ void gpuBlur(unsigned char* image, unsigned char* buffer, int width, int height)
{
    int i = threadIdx.x%width;
    int j = threadIdx.x/width;
    if (i == 0 || j == 0 || i == width - 1 || j == height - 1)
        return;

    int k;
    for (k = 0; k <= 4; k++)
    {
        buffer[4*width*j + 4*i + k] =           (image[4*width*(j-1) + 4*(i-1) + k] +
                                image[4*width*(j-1) + 4*i + k] +
                                image[4*width*(j-1) + 4*(i+1) + k] +
                                image[4*width*j + 4*(i-1) + k] +
                                image[4*width*j + 4*i + k] +
                                image[4*width*j + 4*(i+1) + k] +
                                image[4*width*(j+1) + 4*(i-1) + k] +
                                image[4*width*(j+1) + 4*i + k] +
                                image[4*width*(j+1) + 4*(i+1) + k])/9;
    }
}

int main(int argc, char *argv[])
{
    //Items for image processing;
    //int threshold = 100;
    unsigned int error;
    unsigned char* image;
    unsigned int width, height;

    //Load the image;
    if (argc > 1)
    {
        error = lodepng_decode32_file(&image, &width, &height, argv[1]);
        printf("Loaded file: %s[%d]\n", argv[1], error);
    }
    else
    {

        return 0;
    }

    unsigned char* buffer =(unsigned char*)malloc(sizeof(char) * 4*width*height);

    //GPU Blur Section.
    unsigned char* image_gpu;
    unsigned char* blur_gpu;
    cudaMalloc( (void**) &image_gpu, sizeof(char) * 4*width*height);
    cudaMalloc( (void**) &blur_gpu, sizeof(char) * 4*width*height);
    cudaMemcpy(image_gpu,image, sizeof(char) * 4*width*height, cudaMemcpyHostToDevice);
    cudaMemcpy(blur_gpu,image, sizeof(char) * 4*width*height, cudaMemcpyHostToDevice);
    gpuBlur<<< 1, height*width >>> (image_gpu, blur_gpu, width, height);
    cudaMemcpy(buffer, blur_gpu, sizeof(char) * 4*width*height, cudaMemcpyDeviceToHost);
    //Spit out buffer as an image.
    error = lodepng_encode32_file("GPU_OUTPUT1_Blur.png", buffer, width, height);
    cudaFree(image_gpu);
    cudaFree(blur_gpu);

    free(buffer);
    free(image);

}