0

我制作了一个简单的 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;
         }

    }
4

1 回答 1

2

在对全局内存的越界读取访问的情况下，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-06T00:55:27.267 回答