0

当我创建一个具有 3 深结构的结构并且最深级别有一个 2 维数组时，在使用 CUDA 调试器时分配设备上的内存并访问该数组会导致内存检查器访问冲突错误。这是一个例子：

#include "stdafx.h"

#include <stdio.h>
#include <cuda.h>
#include <cuda_runtime.h>
#include <device_launch_parameters.h>

typedef struct {
    int value;
} Level3;

typedef struct {
    Level3 lvl3ObjArr[10][10];
} Level2;

typedef struct {
    Level2 lvl2Obj;
} Level1;

__global__ void AccessViolationKernel(Level1 *_lvl1Ptr)
{
    int _value;

    _lvl1Ptr->lvl2Obj.lvl3ObjArr[2][5].value = 4;
    _value = _lvl1Ptr->lvl2Obj.lvl3ObjArr[2][5].value;

    printf("Value = %i\n", _value);
}

int _tmain(int argc, _TCHAR* argv[])
{
    Level1 *lvl1Ptr;
    cudaMalloc((void **)&lvl1Ptr, sizeof(Level1));
    AccessViolationKernel<<<5, 1>>>(lvl1Ptr);

    return 0;
}

即使查看内存并添加正确的字节，在使用 CUDA 调试器时，对于 lvl1Ptr 对 lvl3ObjArr[2][5] 的封装引用，一切似乎都是正确的。尽管如此，访问的数据是不正确的，memchecker 会引发访问冲突。

设备上没有正确分配Level1？为什么我会遇到访问冲突？

提前致谢！

-- 更新（2013 年 9 月 30 日下午 16:29 CST）-

此代码编译（对不起！）但它没有显示错误。我认为这是因为我使用的是设备 API malloc 而不是 cudaMalloc，并尝试稍后从主机的 CUDA API 访问数据。我需要一段时间来生成代码来重现它，我很抱歉——我正在减少的源代码是 2800 行长。

4

1 回答 1

0

好的，找到了解决方案。我在内核中将 cudaMalloc 与 malloc/free 混合在一起。这并不直观，因为我使用 cudaMalloc 分配根，然后在使用 malloc 的设备上再次分配它。一些对象仍然通过封装从主机分配，因此设备堆在访问期间不知道，并且会引发访问冲突。

于 2013-10-07T14:58:51.637 回答