3

基本上，我很难准确理解这里出了什么问题。

共享内存在调试时似乎没有以块独占方式运行。正常运行代码时，不会打印任何内容。但是，如果我尝试对其进行调试，则会在块之间共享共享内存并到达 print 语句。

这是一个示例，显然这不是非常有用的代码，但它在我的系统上重现了该问题。难道我做错了什么？这是调试器的错误还是预期行为？

__global__ 
void test()
{
    __shared__ int result[1];
    if (blockIdx.x == 0 && blockIdx.y == 0 && blockIdx.z == 0)
        result[0] = 4444;
    else
    {
        if (result[0] == 4444)
            printf("This should never print if shared memory is unique\n");
    }
}

并启动它：

test<<<dim3(8,8,1), dim3(8,8,1)>>>();

我也完全有可能完全误解了共享内存。

谢谢您的帮助。

其他信息： 我使用的是 GTX 460。为项目设置了 Compute_20 和 sm_20。我正在使用 nsight 3.0 预览版在 Visual Studio 2010 中编写代码。

4

1 回答 1

6

两者之间有一个微妙但重要的区别

块之间共享共享内存并到达打印语句

和

共享内存被连续的块重用并且到达打印语句

你假设前者，但后者是真正发生的事情。

除了第一个块之外，您的代码正在从未初始化的内存中读取。这本身就是未定义的行为。C++（和 CUDA）不保证静态声明的内存在进入或超出范围时设置为任何值。你不能指望它result不会有 4444 的值，尤其是当它可能存储在与可能已将其设置为 4444 值的前一个块相同的共享暂存空间中时。

代码的整个前提和这个问题都是有缺陷的，你不应该从你看到的结果中得出任何结论，即未定义的行为是未定义的。

于 2013-04-02T20:53:38.020 回答