cudaMemcpy函数调用中的"cudaErrorUnknown"

A"cudaErrorUnknown" in cudaMemcpy function call

本文关键字:cudaErrorUnknown 函数调用 cudaMemcpy      更新时间:2023-10-16

我使用一个函数来计算三个向量的矢量点,并使用reduce使其更快。但是,我总是收到这样的错误:

CUDA error at kernel.cu:120 code=30(cudaErrorUnknown) "cudaMemcpy(partia
l_c, dev_partial_c,sizeofblock,cudaMemcpyDeviceToHost )"

我无法弄清楚为什么,因为代码看起来很正常。分配函数没有返回错误。有什么可能的解决方案吗?非常感谢。

double vector_dot(double* d_A,double* d_B,double *d_C,int numElements)
{
    int size = sizeof(double) * numElements;
    int c_size = sizeof(char) * numElements;
    double *d_D=NULL;
    checkCudaErrors(cudaMalloc((void**)&d_D,size)); 
    // Launch the Vector Add CUDA Kernel
    int threadsPerBlock = 256;
    int blocksPerGrid =(numElements + threadsPerBlock - 1) / threadsPerBlock;
    vectorMPL<<<blocksPerGrid, threadsPerBlock>>>(d_A, d_B, d_D, numElements);
    double *partial_c;
    double*dev_partial_c;
    int sizeofblock=blocksPerGrid*sizeof(double);
    partial_c = (double*)malloc(sizeofblock);
    checkCudaErrors( cudaMalloc( (void**)&dev_partial_c,sizeofblock )) ;
    vector_dot_h<<<blocksPerGrid, threadsPerBlock>>>(d_D, d_C, dev_partial_c, numElements);
    double sum = 0;
    checkCudaErrors(cudaMemcpy(partial_c,dev_partial_c,sizeofblock,cudaMemcpyDeviceToHost));
    for (int i=0; i<blocksPerGrid; i++) {
        sum += partial_c[i];
    }
    checkCudaErrors(cudaFree(d_D));
    checkCudaErrors(cudaFree(dev_partial_c));  
    free(partial_c);
    // Reset the device and exit
    checkCudaErrors(cudaDeviceReset());
    return sum;
}

如果我删除它,我将在cudafree调用中收到未知错误。似乎所有 cuda API 调用都无法完成。我想知道为什么?什么是未知的 cuda 错误?原因是什么?

cudaMemcpycudaFree的文档都包含以下注释:

请注意,此函数还可能返回以前的错误代码, 异步启动。

即,错误不是发生在cudaMemcpycudaFree,而是发生在之前的内核启动或执行期间。如果您遵循此建议并将代码修改为如下所示的内容:

vectorMPL<<<blocksPerGrid, threadsPerBlock>>>(d_A, d_B, d_D, numElements);
checkCudaErrors(cudaPeekAtLastError());
checkCudaErrors(cudaDeviceSynchronize());

您应该发现错误是由cudaDeviceSynchronize()调用报告的,指示错误发生在内核执行时。错误的根本原因很可能是vector_dot_h内存访问越界,但由于您没有为有问题的内核调用提供代码和执行参数,因此无法为您提供更准确的诊断。CUDA 工具包附带了一个名为 cuda-memcheck 的实用程序,您可以使用它来获取有关正在运行的内核中非法内存访问模式的更多信息。我建议您尝试在此代码中使用它。

相关文章:
  • 没有找到相关文章