Impossibile compilare il codice che contiene il parallelismo dinamico

Question

Sto eseguendo la programmazione del parallelismo dinamico utilizzando CUDA 5.5 e una NVDIA GeForce GTX 780 con capacità di calcolo pari a 3,5. Sto chiamando una funzione del kernel all'interno di una funzione del kernel, ma mi sta dando un errore:

error : calling a __global__ function("kernel_6") from a __global__ function("kernel_5") is only allowed on the compute_35 architecture or above

Che cosa sto facendo di sbagliato?

Answer 1

È necessario consentire a nvcc di generare codice CC 3.5 per il dispositivo. Questo può essere fatto aggiungendo questa opzione alla linea di comando nvcc.

-gencode arch=compute_35,code=sm_35 

È possibile trovare i campioni CUDA sul parallelismo dinamico per ulteriori dettagli. Contengono sia le opzioni della riga di comando che le impostazioni del progetto per tutti i sistemi operativi supportati.

http://docs.nvidia.com/cuda/cuda-samples/index.html#simple-quicksort--cuda-dynamic-parallelism-

Answer 2

si può fare qualcosa di simile

nvcc -arch=sm_35 -rdc=true simple1.cu -o simple1 -lcudadevrt 

o

Se si dispone di 2 file simple1.cu e test.c allora si può fare qualcosa, come di seguito. Questa è chiamata compilazione separata.

nvcc -arch=sm_35 -dc simple1.cu 
nvcc -arch=sm_35 -dlink simple1.o -o link.o -lcudadevrt 
g++ -c test.c 
g++ link.o simple1.o test.o -o simple -L/usr/local/cuda/lib64/ -lcudart 

Lo stesso è spiegato nel cuda programming guide

Answer 3

Da Visual Studio 2010:

1) View -> Property Pages 
2) Configuration Properties -> CUDA C/C++ -> Common -> Generate Relocatable Device Code -> Yes (-rdc=true) 
3) Configuration Properties -> CUDA C/C++ -> Device -> Code Generation -> compute_35,sm_35 
4) Configuration Properties -> Linker -> Input -> Additional Dependencies -> cudadevrt.lib