Fehler "ungültiges Konfigurationsargument" für den Aufruf des CUDA-Kernels?

Question

Hier ist mein Code:

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"); 

Dies ist die Ausführung meines zweiten Kerns, und es ist in Begriff der Verwendung von Daten völlig unabhängig. BLOCKDIM ist 512, nWidth and nHeight sind auch 512 und cudasafe druckt einfach die entsprechende String-Nachricht des Fehlercodes. Dieser Abschnitt des Codes gibt Konfigurationsfehler direkt nach dem Kernel-Aufruf.

Was könnte diesen Fehler geben, irgendeine Idee?

Answer 1

Diese Art von Fehlermeldung bezieht sich häufig auf die Parameter der Startkonfiguration (Grid/Threadblock-Dimensionen in diesem Fall, könnte in anderen Fällen auch Shared Memory usw. sein). Wenn Sie eine Nachricht wie diese sehen, ist es eine gute Idee, nur Ihre tatsächlichen Konfigurationsparameter auszudrucken, bevor Sie den Kernel starten, um zu sehen, ob Sie irgendwelche Fehler gemacht haben.

sagte Sie BLOCKDIM = 512. Sie haben threadNum = BLOCKDIM/8 so threadNum = 64. Ihre threadblock Konfiguration ist:

dim3 dimBlock(threadNum,threadNum); 

So fragen Sie Blöcke von 64 x 64 Threads zu starten, das heißt 4096 Fäden pro Block. Das funktioniert bei keiner Generation von CUDA-Geräten.

Answer 2

Nur um den vorherigen Antworten hinzuzufügen, können Sie auch die max Fäden erlaubt im Code finden kann, so kann es ohne Hartcodierung die Anzahl der Threads Sie verwenden in anderen Geräten laufen:

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