CUDA Texture2D问题

Question

我很难从二维纹理中提取

texture<float2, cudaTextureType2D, cudaReadModeElementType> tex;
// ...
assert(cudaMallocPitch(&imgcov2_device, &pitch, sizeof(ComplexFloat)*x*y*z, N*N) == cudaSuccess);
cudaChannelFormatDesc channelDesc = cudaCreateChannelDesc<float2>();
tex.addressMode[0] = cudaAddressModeClamp;
tex.addressMode[1] = cudaAddressModeClamp;
tex.filterMode = cudaFilterModePoint;
tex.normalized = false;
assert(cudaBindTexture2D(NULL, tex, imgcov2_device, channelDesc, x*y*z, N*N, x*y*z*N*N*sizeof(ComplexFloat)) == cudaSuccess);
// ...
tmp = ComplexFloatAdd(tmp, ComplexFloatMul(y[j + i*N], tex2D(tex, blockIdx.x * blockDim.x + threadIdx.x, threadIdx.y + j*N))); //fetch

我确信，tex2D的最后2个参数在[0,x*y*z-1]和[0,N*N-1]范围内。在another post中，建议使用高音内存，但我没有运气。有什么想法吗？令人费解的是，当x_y_z = 90000，N_N = 32^2，而N_N = 8^2时，它不会失败。只有提取失败。

Answer 1

当将音调线性存储器绑定到2D纹理时，始终使用cudaMallocPitch返回的音调作为cudaBindTexture2D的最后一个参数。

在你的例子中，你会这样做：

cudaBindTexture2D(NULL, tex, imgcov2_device, channelDesc, x*y*z, N*N, pitch);