內核啓動失敗內核參數的原因

我做了一個簡單的CUDA內核，由於某些原因無法啓動，我不明白。下面你看到我的全球變量。內核啓動失敗內核參數的原因

unsigned int volume[256*256*256];//contains volume data of source 
unsigned int target[256*256*256];//contains volume data of target 
unsigned int* d_volume=NULL;//source data on device 
unsigned int* d_target=NULL;//target data on device

下一個函數是內核啓動器。

void launch_kernel(){ 

cudaMalloc(&d_volume,256*256*256*sizeof(unsigned int)); 
cudaMemcpy(d_volume, volume, 256*256*256*sizeof(unsigned int),cudaMemcpyHostToDevice); 
cudaMalloc(&d_target,256*256*256*sizeof(unsigned int)); 
cudaMemcpy(d_target, target, 256*256*256*sizeof(unsigned int),cudaMemcpyHostToDevice); 
dim3 threads(256,1,1); 
dim3 blocks(256,256,1); 

simple_kernel<<<blocks,threads>>>(d_volume,d_target); 
cudaError_t cudaResult; 
cudaResult = cudaGetLastError(); 
if (cudaResult != cudaSuccess) 
{ 
    cout<<"kernel failed"<<endl; 
} 
cudaMemcpy(volume, d_volume, 256*256*256*sizeof(int),cudaMemcpyDeviceToHost); 
cudaFree(d_volume); 
cudaMemcpy(target, d_target 256*256*256*sizeof(int),cudaMemcpyDeviceToHost); 
cudaFree(d_target); 
}

問題似乎是d_target原因，如果我推出這樣的內核：

simple_kernel<<<blocks,threads>>>(d_volume,d_volume);

它可以正常使用（傳遞到設備必須傳遞的值），並沒有出現任何信息。任何想法爲什麼會發生？內核聲明如下。

__global__ void simple_kernel(unsigned int* src,unsigned int* tgt){ 
//i dont think it matters what it is for. 
     int x = threadIdx.x; 
     int y = blockIdx.x; 
     int z = blockIdx.y; 
     if(x!=0 || x!=255 || y!=0 || y!=255 || z!=0 || z!=255 ){//in bound of memory allocated 
      if(src[x*256*256+y*256+z]==tgt[x*256*256+y*256+z]) 
       if(tgt[(x+1)*256*256+y*256+z]==1 || tgt[(x-1)*256*256+y*256+z]==1 || tgt[(x-1)*256*256+(y+1)*256+z] ||tgt[(x-1)*256*256+(y-1)*256+z]) 
        src[x*256*256+y*256+z]=1; 
       else 
        src[x*256*256+y*256+z]=0; 
     } 

    }

來源

2013-04-06 Philip Xenos

'cudaGetLastError（）'返回的錯誤代碼是什麼？ – stuhlo 2013-04-06 00:24:34

cout << cudaGetErrorString（cudaGetLastError（））<< endl;返回：「沒有錯誤」 – 2013-04-06 00:52:06

「'啓動失敗'是什麼意思？ – stuhlo 2013-04-06 00:56:15

CUDA也可以在超出邊界讀取全局內存的情況下返回錯誤。您在：
if(tgt[(x+1)*256*256+y*256+z]==1 || ...)（例如）中執行這種越界讀取訪問。爲x = y = z = 255哪些經歷您的越界檢查。

在一個情況下，你在出界外的讀取權限啓動您的內核
simple_kernel<<<blocks,threads>>>(d_volume,d_volume);
你真正訪問已經被分配給d_target爲數組d_volume和d_target連續存儲全局內存，因此，沒有錯誤發生。

通過進一步的錯誤檢查或通過cuda-memcheck啓動您的程序來確認我的意見。

來源

2013-04-06 00:55:27 stuhlo

這是問題所在。非常感謝你。 – 2013-04-06 01:07:25

@PhilipXenos不客氣。 – stuhlo 2013-04-06 01:10:33

內核啓動失敗內核參數的原因

回答

相關問題