"błąd nieprawidłowej konfiguracji" dla wywołania jądra CUDA?

Question

Oto mój kod:

int threadNum = BLOCKDIM/8; 
dim3 dimBlock(threadNum,threadNum); 
int blocks1 = nWidth/threadNum + (nWidth%threadNum == 0 ? 0 : 1); 
int blocks2 = nHeight/threadNum + (nHeight%threadNum == 0 ? 0 : 1); 
dim3 dimGrid; 
dimGrid.x = blocks1; 
dimGrid.y = blocks2; 

// dim3 numThreads2(BLOCKDIM); 
// dim3 numBlocks2(numPixels/BLOCKDIM + (numPixels%BLOCKDIM == 0 ? 0 : 1)); 
perform_scaling<<<dimGrid,dimBlock>>>(imageDevice,imageDevice_new,min,max,nWidth, nHeight); 
cudaError_t err = cudaGetLastError(); 
cudasafe(err,"Kernel2"); 

Jest to realizacja mojego drugiego jądra i jest w pełni niezależny w perspektywie wykorzystania danych. BLOCKDIM to 512, nWidth and nHeight to także 512, a cudasafe po prostu drukuje odpowiednią wiadomość z kodem błędu. Ta sekcja kodu podaje błąd konfiguracji tuż po wywołaniu jądra.

Co może dać ten błąd, jakiś pomysł?

Answer 1

Ten typ komunikatu o błędzie często odnosi się do parametrów konfiguracji uruchamiania (wymiary grid/threadblock w tym przypadku mogą być również pamięcią wspólną itd. W innych przypadkach). Kiedy zobaczysz taki komunikat, dobrym pomysłem jest wydrukowanie rzeczywistych parametrów konfiguracyjnych przed uruchomieniem jądra, aby sprawdzić, czy popełniłeś jakieś błędy.

Mówiłeś BLOCKDIM = 512. Trzeba threadNum = BLOCKDIM/8 tak threadNum = 64. Konfiguracja threadblock jest:

dim3 dimBlock(threadNum,threadNum); 

Więc prosicie, aby uruchomić bloki 64 x 64 wątków, czyli 4096 wątków na blok. To nie zadziała na żadnej generacji urządzeń CUDA.

Answer 2

Wystarczy dodać do poprzednich odpowiedzi, można znaleźć wątki max dopuszczalne w kodzie też, więc można go uruchomić w innych urządzeniach bez sztywnego kodowania liczbę wątków będzie użyć:

struct cudaDeviceProp properties; 
cudaGetDeviceProperties(&properties, device); 
cout<<"using "<<properties.multiProcessorCount<<" multiprocessors"<<endl; 
cout<<"max threads per processor: "<<properties.maxThreadsPerMultiProcessor<<endl;