すべてのアクセスをCUDAのグローバルメモリに向けるにはどうすればよいですか？

Question

プログラムからのすべてのアクセスが（L1/L2キャッシュにデータが見つかったとしても）グローバルメモリにアクセスしたい。

-Xptxas -dlcm=cg 

CUDAドキュメントの状態この：このために私は、L1キャッシュがコンパイラNVCCするには、これらのオプションを渡すことでスキップすることができることが分かったので、

.cv Cache as volatile (consider cached system memory lines stale, fetch again). 

を、私はどちらかで実行するとき、私は想定しています - dlcm = cgまたは-dlcm = cvの場合、生成されるPTXファイルは正常に生成されたファイルとは異なるはずです。 （負荷が.cgまたは.cvのいずれかを付加する必要があります）

私のサンプルプログラム：

__global__ void rh_kernel(int *datainRowX, int *datainRowY) { 
    int tid = blockIdx.x * blockDim.x + threadIdx.x; 
    if (tid != 0) 
     return; 
    int i, x, y; 
    x = datainRowX[1]; 
    y = datainRowY[2]; 
    datainRowX[0] = x + y; 
} 

int main(int argc, char** argv) { 
    int* d_datainRowX; 
    cudaMalloc((void**)&d_datainRowX, sizeof(int) * 268435456); 

    int* d_datainRowY; 
    cudaMalloc((void**)&d_datainRowY, sizeof(int) * 268435456); 

    rh_kernel<<<1024, 1>>>(d_datainRowX, d_datainRowY); 
    cudaFree(d_datainRowX); cudaFree(d_datainRowY); 
    return(0); 
} 

が、私は何のオプション私はNVCCコンパイラに渡すことに注意してください（「-Xptxas -dlcm = CG」または"-Xptxas -dlcm = cv"または何もない）、生成されたPTXの3つのケースすべてで同じです。私はPTXファイルを生成するために-ptxオプションを使用しています。 私は何が欠けていますか？私がやっていることを達成するための他の方法はありますか？ お時間をいただきありがとうございます。 Cuda Toolkit Documentationによれば

Answer 1

：

ケプラーのGPUにおけるL1キャッシュは、ローカルメモリ用に予約されているが、そのようなレジスタスピルとスタックデータとして にアクセスします。グローバルロードはL2 （または読み取り専用データキャッシュ）にのみキャッシュされます。そのようなテスラK40 GPUアクセラレータ、GK20A、 とGK210として

GK110Bベースの製品

L1キャッシュは、グローバルメモリには使用されないデフォルトでは、この動作を保持するデフォルトでケプラーに読み出します。したがって、-Xptxas -dlcm=cgを追加すると、PTXに違いはありません。

L2キャッシュを無効にすることはできません。