c - Cudamalloc 的神秘段错误

Question

谁能帮我理解为什么下面的代码会导致段错误？同样，谁能帮助我理解为什么将标记为“坏”的两条线换成标记为“好”的两条线不会导致段错误？

请注意，段错误似乎发生在 cudaMalloc 行；如果我评论出来，我也看不到段错误。这些分配似乎相互踩踏，但我不明白如何。

代码的意图是设置三个结构:主机上的 h_P，它将由 CPU 例程填充设备上的 d_P，它将由 GPU 例程填充h_P_copy 在主机上，将通过复制 GPU 数据结构来填充。

这样我就可以验证正确的行为并对比另一个基准。
事实上，所有这些都是四维数组。

(如果有关系，该卡是 GTX 580，在 SUSE Linux 下使用 nvcc 4.2)

#define NUM_STATES              32
#define NUM_MEMORY              16

int main( int argc, char** argv) {

        // allocate and create P matrix
        int P_size      = sizeof(float) * NUM_STATES * NUM_STATES * NUM_MEMORY * NUM_MEMORY;
        // float *h_P      = (float*) malloc (P_size);  **good**
        // float *h_P_copy = (float*) malloc (P_size);  **good**
        float h_P[P_size];                            //  **bad**
        float h_P_copy[P_size];                       //  **bad**
        float *d_P;
        cudaMalloc( (void**) &d_P, P_size);
        cudaMemset( d_P, 0.0, P_size);

}

Answer 1

这可能是由于某种堆栈损坏造成的。

注意事项:

• “好”行从系统堆中分配，“坏”行分配堆栈存储空间。
• 通常你可以从栈中分配的数量是相当多的小于您可以从堆中分配的内容。
• “好”和“坏”声明保留的金额不同float 存储。 “坏”正在分配 4 倍的 float存储。
• 最后，cudaMemset，就像 memset 一样，正在设置 bytes 和需要一个 unsigned char 数量，而不是一个 float (0.0) 数量。

由于 cudaMalloc 行是第一个在“坏”情况下实际“使用”(尝试设置)任何已分配堆栈存储的行，因此它是发生段错误的地方。如果您像这样添加了额外的声明:

    float *d_P;
    float myval;  //add
    myval = 0.0f; //add2
    cudaMalloc( (void**) &d_P, P_size);

我怀疑您可能会看到段错误发生在“add2”行上，因为它会首先使用损坏的堆栈存储。