gcc - 创建 CUDA 共享库和 libpthread 的问题

Question

我目前正在尝试使用 CUDA 例程创建一个库，但我遇到了麻烦。我将使用一个相当简单的示例来解释我的问题，我的实际库会更大。

我已经写成功了test.cu ，包含 __global__ 的源文件CUDA 函数及其周围的包装器(用于分配和复制内存)。我还可以使用以下命令成功将此文件编译到共享库中:

nvcc -c test.cu -o test.o -lpthread -lrt -lcuda -lcudart -Xcompiler -fPIC
gcc -m64 -shared -fPIC -o libtest.so test.o -lpthread -lrt -lcuda -lcudart -L/opt/cuda/lib64

结果 libtest.so导出所有我需要的符号。

我现在编译我的纯 C main.c并将其链接到我的库:

gcc -std=c99 main.c -o main -lpthread -ltest -L.

这一步也成功了，但是在执行 ./main所有被调用的 CUDA 函数都返回错误:

test.cu:17:cError(): cudaGetDeviceCount: [38] no CUDA-capable device is detected
test.cu:17:cError(): cudaMalloc: [38] no CUDA-capable device is detected
test.cu:17:cError(): cudaMemcpy: [38] no CUDA-capable device is detected
test.cu:17:cError(): cudaMemcpy: [38] no CUDA-capable device is detected
test.cu:17:cError(): cudaFree: [38] no CUDA-capable device is detected

(错误消息是通过我自己的调试功能创建的)

在我最初的步骤中，我遇到了完全相同的问题，因为我直接从 test.cu 创建了一个可执行文件。 ，因为我忘记链接 libpthread ( -lpthread )。但是，正如您在上面看到的，我已经将所有源文件链接到 libpthread。根据 ldd , 两个 libtest.so和 main取决于 libpthread，因为它应该是。

我在 ArchLinux 上使用 CUDA 5(是的，我确实意识到它是一个测试版)和 gcc 4.6.3 和 nvidia 驱动程序版本 302.06.03。

解决这个问题的一些帮助将不胜感激!

Answer 1

这是一个简单的例子......

// File: test.cu
#include <stdio.h>

__global__ void myk(void)
{
    printf("Hello from thread %d block %d\n", threadIdx.x, blockIdx.x);
}

extern "C"
void entry(void)
{
    myk<<<1,1>>>();
    printf("CUDA status: %d\n", cudaDeviceSynchronize());
}

编译/链接 nvcc -m64 -arch=sm_20 -o libtest.so --shared -Xcompiler -fPIC test.cu .

// File: main.c
#include <stdio.h>

void entry(void);

int main(void)
{
    entry();
}

编译/链接 gcc -std=c99 -o main -L. -ltest main.c .