3

我最近开始学习 CUDA，我偶然发现了一个我无法理解的非常奇怪的行为。

我的代码本质上计算了一个简单 atomicAdd 内核的平均执行时间。为此，我在循环中调用内核以获得更好的平均值。我将设备内存分配和副本包含在循环中，因为我想将其包含在我的执行时间估计中。问题是，如果循环的运行次数过多，程序通常会失败并出现 Runtime API 错误 30。

我怀疑我的内存访问可能有问题，所以我在程序上运行 memcheck 无济于事。显然没有内存错误。此外，如果只运行内核几次，就没有问题，这似乎也表明内核并不是问题所在。只有连续调用太频繁才会有问题。

我的代码框架如下：

for(int i = 0; i < runs; i++)
{


    //////////////////////////////////
    // Copy memory from Host to Device
    //////////////////////////////////

    cutilSafeCallNoSync( cudaMemcpy(dev_waveforms, waveforms, num_wf * wf_length *  sizeof(float), 
                        cudaMemcpyHostToDevice) );
    cutilSafeCallNoSync( cudaMemcpy(dev_delays, delays, num_wf * sizeof(int), 
                        cudaMemcpyHostToDevice) );




    ////////////////////////
    // Kernel Call
    ////////////////////////

    kernel_wrapper<float>(dev_waveforms, dev_focused, dev_delays, 
                    wf_length, num_wf, threads, blocks, kernel); 

    //copy back to host memory.
    cutilSafeCallNoSync( cudaMemcpy(focused, dev_focused, J * wf_length * sizeof(float), 
        cudaMemcpyDeviceToHost) );

}

同样，这仅在运行足够大时才会失败。还有其他一些奇怪的事情发生了，但我现在就暂且不说。

哦，我正在使用 Visual Studio 2010 在 Windows 7 上进行开发。我的 GPU 还充当我的视频卡，我担心这可能会产生奇怪的效果。

提前致谢！

4

3 回答 3

2

Windows 7 驱动程序可以将多个命令批处理到单个提交中，以规避 WDDM 增加的驱动程序开销（与 WDDM 之前的驱动程序相比，例如 Win XP）。出于这个原因，即使单个内核没有超过看门狗，在这样的循环中运行也可能。您可以调用cudaDeviceSynchronize()@RogerDahl 建议尝试解决它（可能只有每 N 次迭代）。

或者在 Linux 上运行。

编辑： 运行时错误 30 是一个未知错误。如果这是看门狗定时器超时，我预计会出现cudaErrorLaunchTimeout（错误 6）。由于您没有提供完整的代码，因此很难说是什么导致了错误。我怀疑您的内核代码中存在错误。

于 2012-08-31T04:45:35.527 回答
1

我遇到了同样的错误，发现我的内核实际上超出了我分配的内存。由于您将缓冲区加倍并看到问题消失，我希望您可能会遇到同样的问题。

我的问题是我的数学中的一个错误，以确定要启动多少线程和块。我发射的区块数量是我预期的八倍。在我的内核中，确定给定线程应该处理哪个元素的数学运算导致访问我的数组之外的方式。

确保检查每个线程正在使用数组的哪些元素，以防止执行将访问/修改数组外内存的线程。

于 2013-01-15T16:53:59.340 回答
1

对于其他来此帖子寻找答案的人，为什么您会收到错误 30 消息：

如果您不小心将 CPU 变量作为 GPU设备函数的参数之一，也会出现此错误。这对我来说是这个问题的最常见原因。在多次意外地将变量的 cpu 副本作为参数放置之后，您会想，但是......

确保设备函数的所有参数： myDeviceFunciont<<<1,N>>>(argument1, argument2, argument3)

是 GPU 变量（即：您在 cudaMalloc 和 cudaMemcpy 中用于在 GPU 上分配内存的变量）

于 2013-04-12T15:56:39.030 回答