CUDA-GDB:无CUDA设备

Question

我正在尝试调试一个源代码，它工作得很好，并且在编译时不会出现错误或警告。问题是，当我使用cuda-gdb一步一步地运行它时，根本没有启动CUDA内核(我从调试器得到的输出与Nvidia cuda-gdb指南中显示的完全不同)，但程序仍然可以正常工作，没有任何错误。在任何时候我都得不到CUDA内核、设备或线程。显然，焦点也没有放在任何事情上。我使用的是CUDA-GDB的4.2版本。

这是我在调试器应该启动内核时得到的结果：

Breakpoint 1, matrixMulGPU (M=0x609160, N=0x609270, P=0x609490, Width=8)
    at matrixMul1.cu:141
141     MatrixMulKernel<<<dimGrid, dimBlock>>>(Md, Nd, Pd, Width);
(cuda-gdb) step
MatrixMulKernel (__cuda_0=0x210000, __cuda_1=0x210100, __cuda_2=0x210200, 
    __cuda_3=8) at matrixMul1.cu:103
103 __global__ void MatrixMulKernel(float *Md, float *Nd, float *Pd, int Width){
(cuda-gdb) step
__device_stub__Z15MatrixMulKernelPfS_S_i (__par0=0x210000, __par1=0x210100, 
    __par2=0x210200, __par3=8)
    at tmpxft_000016d4_00000000-1_matrixMul1.cudafe1.stub.c:5
5   tmpxft_000016d4_00000000-1_matrixMul1.cudafe1.stub.c: Arquivo ou diretório não encontrado.
    in tmpxft_000016d4_00000000-1_matrixMul1.cudafe1.stub.c
(cuda-gdb) step
cudaLaunch<char> (
    entry=0x4011ea "UH\211\345SH\203\354(H\211}\350H\211u\340H\211U؉MԋM\324H\213U\330H\213]\340H\213E\350H\211\336H\211\307\350\024\377\377\377H\203\304([\311\303UH\211\345SH\203\354(\277Pn@") at cuda_runtime.h:958
958   return cudaLaunch((const char*)entry);
(cuda-gdb) step
959 }
(cuda-gdb) step
MatrixMulKernel (__cuda_0=0x210000, __cuda_1=0x210100, __cuda_2=0x210200, 
    __cuda_3=8) at matrixMul1.cu:121
121 }

我的CUDA设备是GeForce 8400M GS，我的deviceQuery检查没有问题。我不知道如何解决这个问题，因为Nvidia论坛这几天离线了！

在此之前非常感谢。

Answer 1

查看cuda-gdb输出，您似乎是在内核启动的主机组件(即<<< >>>)上。CUDA内核的启动是异步的。主机调用准备启动，并将在它完成之前返回(或者在某些情况下甚至在启动的工作开始之前)。因此，当您在主机上停止时，启动的工作可能尚未调度到GPU。

进入主机端内核启动调用将不会进入设备上的内核启动。取而代之的是，尝试在内核内部设置一个断点，让应用程序自由运行。断点可以通过文件:行号(例如break matrixMul1.cu:<line> )或名称(例如break MatrixMulKernel)来设置。当命中设备端断点时，cuda-gdb将返回到提示并根据需要将焦点设置在设备上。