2

在我当前的项目中，一个电话cudaGetLastError()正在返回unknown error，我不知道为什么。代码编译得很好，但它的行为不像我想要的那样。

下面是一个简短的、不可编译的示例，说明相关代码的组成：

CU_Main.cu

下面是 CUDA 内核：

//My CUDA kernel
__global__ void CU_KernelTest(Kernel* matrix){
    int idx = blockIdx.x * blockDim.x + threadIdx.x;  
    int idy = blockIdx.y * blockDim.y + threadIdx.y;  

    if(idx == 0 && idy == 0){
            printf("ID is: %d\n", idx);
            matrix->set(1,1, 16.0f);
    }
}

这是主机代码：

//A host function which is called when a button is clicked
int HOST_OnbuttonClick(){
    Kernel* matrix = new Kernel(3,3,2);
    Kernel* device_matrix;

    cudaMalloc(&device_matrix, sizeof(Kernel));
    cudaMemcpy(device_matrix, matrix, sizeof(Kernel), cudaMemcpyHostToDevice);

    CU_KernelTest<<<256, 256>>>(device_matrix);
    cudaDeviceSynchronize();

    cudaError_t err = cudaGetLastError();
    if (err != cudaSuccess) {
        printf("Error: %s\n", cudaGetErrorString(err));
    }


    cudaFree(device_matrix);
    return 0.0f;
}

当matrix->set(1,1, 16.0f);被包含在 cuda 内核中时，(err != cudaSuccess)返回 true 并打印出来UNKNOWN ERROR，而如果我注释掉set，我不会收到错误。

与此相关的另一个struct是我自己的卷积核设计助手，自然称为Kernel.

内核.cuh

struct Kernel {
    private :
        float* kernel;
        int rows;
        int columns;

    public :

        __device__ __host__
        Kernel(int _rows, int _columns, float _default) {
            rows = _rows;
            columns = _columns;
            kernel = new float[rows * columns];

            for(int r = 0; r < rows; r++){
                for(int c = 0; c < columns; c++){
                    kernel[r * rows + c] = _default;
                }
            }
        }

        __device__ __host__
        void set(int row, int col, float value){
            kernel[row * rows + col] = value;
        }
}

此设计的目标是能够为主机上的内核设置所有值，将其发送到 CUDA 内核，在那里设置值，然后在主机上检索更新的对象。

所以，真的有两个问题，为什么我会收到一条unknown error消息，代码在语法上是否正确，它应该可以工作？如果需要更多信息，请告诉我。

以下是内存检查器的结果：

Nsight Debug
================================================================================
CUDA Memory Checker detected 1 threads caused an access violation:
Launch Parameters
    CUcontext    = 071c7340
    CUstream     = 08f3e3b8
    CUmodule     = 08fa97a8
    CUfunction   = 08fdbbe8
    FunctionName = _Z13CU_KernelTestP6Kernel
    gridDim      = {1,1,1}
    blockDim     = {256,1,1}
    sharedSize   = 128
    Parameters:
        matrix = 0x06b60000  {kernel = 0x07a31718  ???, rows = 3, columns = 3}
    Parameters (raw):
         0x06b60000
GPU State:
   Address  Size      Type  Mem       Block  Thread         blockIdx  threadIdx      PC  Source
-----------------------------------------------------------------------------------------------
  07a31728     4    adr st    g           0       0          {0,0,0}    {0,0,0}  000260  c:\users

Summary of access violations:
c:\users....kernel.cuh(26): error MemoryChecker: #misaligned=0  #invalidAddress=2
4

1 回答 1

2

您的Kernel类包含一个指针。将类复制到设备时，设备上有一个主机指针。在设备上取消引用它会给你这个无效的地址访问冲突。

这似乎是造成混乱的常见原因。罗伯特·克罗维拉昨天刚刚解释过。

于 2013-04-16T21:01:10.487 回答