cuda - CUDA 1D テクスチャ フェッチは常に 0 を返す

Question

簡単なコードで CUDA 1D テクスチャをテストしようとしています。これは非常に簡単です。最初にグローバル メモリを割り当て、次にそれをテクスチャ リファレンスにバインドします。tex1D() によってカーネル内からテクスチャにアクセスします。テクスチャ フェッチによって返された値を出力します。

コードは次のとおりです。

#include "cuda.h"
#include "cuda_runtime.h"
#include <iostream>
#include <vector>
#include <cstdio>

using namespace std;

texture<float, cudaTextureType1D, cudaReadModeElementType> texX;

__global__ void kernel(float *X)
{
    int i = threadIdx.x ;
    if ( i >= 128 ) return;
    printf("%.3f\t%.3f\n", tex1D( texX, i*1.0 ), X[i] );
}

int main()
{
    float *devX;
    vector<float> X(128, 3.1415926 );
    cudaMalloc( &devX, 128 * sizeof(float) );
    cudaMemcpy( devX, &X[0], 128*sizeof(float), cudaMemcpyDefault );
    cudaDeviceSynchronize();

    cudaBindTexture( (size_t)0, texX, devX, 128 * sizeof(float) );
    cudaDeviceSynchronize();

    kernel<<<1,128>>>( devX );
    cudaDeviceSynchronize();
    cout<<endl;
    cout<< cudaGetErrorString( cudaGetLastError() ) <<endl;
}

しかし、私が得たのは次のようなものだけでした：

0.000    3.142
0.000    3.142
...
0.000    3.142

no error

誰でも理由を説明できますか？

Answer 1

tex1Dfetch()テクスチャは線形メモリにバインドされているため、使用する必要があります。

printf("%.3f\t%.3f\n", tex1Dfetch( texX, i ), X[i] );