cuda中的纹理内存 二维纹理绑定错误

在CUDA初学者的旅程中,遇到一个由于二维纹理内存绑定导致的bug,耗费了两天时间调试。问题在于将设备指针与二维纹理绑定后,解引用的值与纹理内存fetch的值不一致。经过研究发现,线性内存(全局内存)只能与一维纹理绑定,而二维纹理需要CUDA Array。虽然某些示例中线性内存与二维纹理绑定能工作,但当线性内存大小不是2的n次幂且维度不同时,会出现问题。解决办法是确保每个维度大小为2的n次幂且相等,以便GPU能更高效地读取内存。
摘要由CSDN通过智能技术生成

        初学cuda,受了很多罪。因为在windows开发环境中,图形界面占用了很多gpu资源,因此从用了四年的vs转战到linux下的vim+nvcc+cuda-gdb。对用习惯了随手加断点,随便添监视的vs忠实用户来说,这个没有可视化、没有集成的开发环境实在是有点不习惯。再加上对于gpu程序初次接触,因此造成了开发时间的极大浪费。

        一个bug,让我调了整整两天。

        这个bug是这样的:我定义了一个设备指针,申请了一块global memory,又将该指针与一个纹理内存绑定,但是指针解引用的值与对应的纹理内存fetch的值不一致。因为我自认这个做法是按照《GPU高性能编程 CUDA实战》第七章 纹理内存 的example来的,因此很是不解(其实用过CUDA或者opengl纹理的人,可能一下就能想到是绑定纹理出了问题)。


        为什么出问题?原因就在于我使用了二维纹理。根据http://www.opengpu.org/forum.php?mod=viewthread&tid=670这篇文章的描述。linear memory(我理解的就是普通的global memory)只能与一维纹理绑定,只有CUDA Array才能与二维纹理和三维纹理绑定。但是上述书籍中的实例,linear memory与二维纹理绑定的例子确实也在用。但为什么我的代码就会出问题呢?

        直接宣布答案:当使用linear memory与二维纹理绑定时,每一维的大小必须都是2的n次幂,

  • 0
    点赞
  • 0
    收藏
    觉得还不错? 一键收藏
  • 0
    评论
CUDA使用二维数组需要进行以下步骤: 1. 在主机端(CPU端)定义一个二维数组,例如: ``` int h_array[N][M]; ``` 其N和M分别代表数组的行数和列数。 2. 在设备端(GPU端)定义一个指针,指向这个二维数组的首地址,例如: ``` int (*d_array)[M]; ``` 这里使用了指针数组的方式,因为二维数组在内存是按行存储的,指针数组可以方便地实现这种存储方式。 3. 在CUDA核函数,将主机端的数组拷贝到设备端: ``` cudaMemcpy(d_array, h_array, N * M * sizeof(int), cudaMemcpyHostToDevice); ``` 这里使用了CUDA提供的数据拷贝函数`cudaMemcpy`,将主机端的数组`h_array`拷贝到设备端的数组`d_array`。 4. 在CUDA核函数,可以使用二维数组进行计算,例如: ``` __global__ void kernel(int (*array)[M]) { int i = blockIdx.x * blockDim.x + threadIdx.x; int j = blockIdx.y * blockDim.y + threadIdx.y; if (i < N && j < M) { array[i][j] = i * j; } } ``` 这里使用了CUDA二维块和二维线程的概念,将二维数组的每个元素计算出来。 5. 在CUDA核函数执行完毕后,将设备端的数组拷贝回主机端: ``` cudaMemcpy(h_array, d_array, N * M * sizeof(int), cudaMemcpyDeviceToHost); ``` 这里使用了CUDA提供的数据拷贝函数`cudaMemcpy`,将设备端的数组`d_array`拷贝回主机端的数组`h_array`。 以上就是在CUDA使用二维数组的基本步骤。需要注意的是,在定义二维数组的时候,数组的行数和列数必须是常量,不能是变量。
评论
添加红包

请填写红包祝福语或标题

红包个数最小为10个

红包金额最低5元

当前余额3.43前往充值 >
需支付:10.00
成就一亿技术人!
领取后你会自动成为博主和红包主的粉丝 规则
hope_wisdom
发出的红包
实付
使用余额支付
点击重新获取
扫码支付
钱包余额 0

抵扣说明:

1.余额是钱包充值的虚拟货币,按照1:1的比例进行支付金额的抵扣。
2.余额无法直接购买下载,可以购买VIP、付费专栏及课程。

余额充值