是否有相当于perror()的CUDA？

Question

是否有一个CUDA函数用于打印调用者提供的错误消息和描述当前cudaStatus (或调用者提供的cudaStatus)的错误消息，a-la-perror()

Answer 1

我不认为有一个内置的cuda API函数可以做到这一点。

此宏将执行您所描述的操作：

#define cudaCheckErrors(msg) \
    do { \
        cudaError_t __err = cudaGetLastError(); \
        if (__err != cudaSuccess) { \
            fprintf(stderr, "Fatal error: %s (%s at %s:%d)\n", \
                msg, cudaGetErrorString(__err), \
                __FILE__, __LINE__); \
            fprintf(stderr, "*** FAILED - ABORTING\n"); \
            exit(1); \
        } \
    } while (0)

上面宏的用法只是将其插入到任何cuda API调用或任何cuda内核调用之后。建议在每次cuda API调用和内核调用后插入，例如：

cudaMemcpy(d_A, A, sizeof(A), cudaMemcpyHostToDevice);
cudaCheckErrors("cudaMemcpy fail");
my_kernel<<<blocks, threads>>>(d_A);
cudaCheckErrors("kernel launch fail");
cudaDeviceSynchronize();
cudaCheckErrors("cudaDeviceSynchronize fail");

它打印用户定义的消息(msg)，还解码cuda API错误并打印相应的错误字符串消息：

Fatal error: kernel launch fail (invalid configuration argument at t128.cu:44)
*** FAILED - ABORTING

您可能还会对错误处理here的讨论感兴趣。

为了回答下面的问题，您可以轻松地创建一个函数调用版本：

void cudaCheckErrors(char *msg){
        cudaError_t __err = cudaGetLastError(); \
        if (__err != cudaSuccess) { fprintf(stderr, "Fatal error: %s (%s at %s:%d)\n", msg, cudaGetErrorString(__err),  __FILE__, __LINE__);
            fprintf(stderr, "*** FAILED - ABORTING\n");
            exit(1);
        }
}