創建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出口我所有需要的符號。

現在我編譯我的純粹ç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上使用gcc 4.6.3和nvidia驅動程序版本302.06.03使用CUDA 5（是的，我意識到它是一個測試版）。

有些幫助解決這個問題將不勝感激！

Answer 1

這裏有一個簡單的例子......與nvcc -m64 -arch=sm_20 -o libtest.so --shared -Xcompiler -fPIC test.cu

// 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()); 
} 

編譯/鏈接。

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

void entry(void); 

int main(void) 
{ 
    entry(); 
} 

編譯/鏈接gcc -std=c99 -o main -L. -ltest main.c。