PTX kernel name mangling

Oct 03 2020

ptxDosyadan bir çekirdek derlendiğinde Cuda programımı bağlayamıyorum .

main.cu:

extern 
__global__ void kernel(int, float*);

int main()
{
    ...
    kernel<<<...>>>(...);
    ...
}

kernel.cu

__global__
void kernel(int n, float* p)
{
    ...
}

Aşağıdaki gibi derlersem sorunum olmaz ve çalıştırılabilir bir dosya alırım:

nvcc -dc main.cu kernel.cu --gpu-architecture=sm_70
nvcc -dlink main.o kernel.o --gpu-architecture=sm_70 -o dlink.o
g++ dlink.o main.o kernel.o -lcudart

Aşağıdaki gibi derlersem (oluşturarak ptx), hatalar alıyorum:

nvcc -ptx kernel.cu --gpu-architecture=sm_70
nvcc -dc main.cu kernel.ptx --gpu-architecture=sm_70
nvcc -dlink main.o kernel.o --gpu-architecture=sm_70 -o dlink.o
g++ dlink.o main.o kernel.o -lcudart

Hata:

main.o: In function `main':
tmpxft_0000b5ce_00000000-5_main.cudafe1.cpp:(.text+0x4789): undefined reference to `kernel(int, float*)'
tmpxft_0000b5ce_00000000-5_main.cudafe1.cpp:(.text+0x497e): undefined reference to `kernel(int, float*)'
collect2: error: ld returned 1 exit status

Bir örnek takip ediyorum CUDA_Compiler_Driver_NVCC.pdf.

Hatayı düzeltmek için ne yapmam gerekiyor?

(Bu CUDA 10.2'dir).

Yanıtlar

2 RobertCrovella Oct 02 2020 at 23:46

Kendi PTX'inizi yazmak (veya PTX'i değiştirmek) istiyorsanız, kullanılacak uygun CUDA metodolojisi CUDA sürücü API'si ve ilgili derleme akışıdır.

CUDA vectorAddDrv örnek kodu , ihtiyacınız olan tüm tesisat ve iş akışına sahiptir.