Ошибка компиляции кода с динамическим параллелизмом

Question

Я занимаюсь программированием динамического параллелизма с использованием CUDA 5.5 и NVIDIA GeForce GTX 780, вычислительная способность которого равна 3,5. Я вызываю функцию ядра внутри функции ядра, но это дает мне ошибку:

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

Что я делаю неправильно?

Answer 1

Необходимо, чтобы nvcc генерировал код CC 3.5 для вашего устройства. Это можно сделать, добавив эту опцию в командную строку nvcc.

-gencode arch=compute_35,code=sm_35 

Вы можете найти образцы CUDA для динамического параллелизма для более подробной информации. Они содержат как параметры командной строки, так и параметры проекта для всех поддерживаемых ОС.

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

Answer 2

Вы можете сделать что-то вроде этого

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

или

Если у вас есть 2 файла simple1.cu и test.c, то вы можете сделать что-то, как показано ниже. Это называется отдельной компиляцией.

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 

То же объясняется в cuda programming guide

Answer 3

С 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