スタティックマトリックスがcudaMemCpyToSymbolに渡されました

Question

静的に割り当てられたマトリックスで定数メモリを使用したいと思います。

float h_M[MASK_WIDTH][MASK_WIDTH] = { 
    { 1, 2, 3, 2, 1 }, 
    { 2, 3, 4, 3, 2 }, 
    { 3, 4, 5, 4, 3 }, 
    { 2, 3, 4, 3, 2 }, 
    { 1, 2, 3, 2, 1 } 
}; 

そして、私は次の関数にh_M行列を渡す必要があります：次のようにmain()機能で

#define MASK_WIDTH 5 
#define MAX_MASK_WIDTH 10 
__constant__ float M[MAX_MASK_WIDTH][MAX_MASK_WIDTH]; 

は、静的に割り当てられた行列を持っている：私は次のように定数行列を宣言

cudaMemcpyToSymbol(M, h_M, sizeof(h_M)); 

これは、で定義されています。cudaMemCpyToSymbol

どうすれば正しく行うことができますか？行列を特定の値で初期化する必要があることを考慮して、それを宣言して動的に割り当てることはできないと思います。 cudaMemCopytosymbolは、コピー後にすべての値がMの0の場合、影響がありません。

あなたは完全なソースコードが必要な場合、それは次のリンクである：このようにcached_convolution_2D_basic

Answer 1

：

あなたが壊れているものを

cudaMemcpyToSymbol(M, h_M, MASK_WIDTH*MASK_WIDTH*sizeof(float)); 

：

cudaMemcpyToSymbol(M, h_M, sizeof(sizeMask_Width)); 

sizeof(sizeMask_Width)を求めていますコンパイラ "sizeMask_Widthと呼ばれる変数のサイズは何ですか？それはint変数ですので、答えはです。その呼び出しは4バイトしか転送しません。 sizeMask_Widthあなたが転送する必要があるバイトの実際の正しい数であるMASK_WIDTH*MASK_WIDTH*sizeof(float)と同じであるため、

cudaMemcpyToSymbol(M, h_M, sizeMask_Width); 

：あなたはこれを行っている必要があります。

あなたのケースではsizeof(h_M)も同様に働いていたと思いますが、将来の読者のためには、h_Mの特定の定義に依存しています。それは他のわずかに異なる場合にはうまくいかないかもしれません。

Answer 2

問題[解決] 問題は、私が代わりに生の主要なレイアウトの行列レイアウトとして考えたということでした。 下の画像を見る

Mアレイサイズを有する：MASK_WIDTH * MASK_WIDTH：MAX_MASK_WIDTH * MAX_MASK_WIDTHは、代わりh_Mアレイサイズを有します。ですから、私はcudaMemCpyToSymbol関数を呼び出すと、h_M行列を生の主要なレイアウト順でM行列にコピーします。 一つは、さまざまな方法で問題を解決することができる：

1. それが最初にあったように、異なる寸法を有する一次元 ベクトルとして（この場合）Mとh_M両方matriciesを宣言する同じ寸法
2. の行列を宣言したが、カーネルコードに M[i * MASK_WIDTH + j]を使用してください。