このページの内容は最新ではありません。最新版の英語を参照するには、ここをクリックします。

gpucoder.atomicSub

指定された値のグローバル メモリまたは共有メモリの変数からのアトミックな減算

R2021b 以降

ページ内をすべて折りたたむ

    構文

    [A,oldA] = gpucoder.atomicSub(A,B)

    説明

    [A,oldA] = gpucoder.atomicSub(A,B) は、B をグローバル メモリまたは共有メモリの A の値から減算し、結果を A に書き戻します。この演算は、読み取り、変更、書き込みの操作全体が他のスレッドからの干渉なしに実行されることが保証されているという意味でアトミックです。入力引数と出力引数の順序は、構文の規定と一致しなければなりません。

    例

    例

    すべて折りたたむ

    関数 gpucoder.atomicSub を使用してシンプルなアトミック減算演算を実行し、対応する CUDA® atomicSub() API を呼び出す CUDA コードを生成します。

    1 つのファイル内に、行列入力 a および b を受け入れるエントリポイント関数 myAtomicSub を記述します。

    function a = myAtomicSub(a,b)

coder.gpu.kernelfun;
for i = 1:numel(a)
    [a(i),~] = gpucoder.atomicSub(a(i),b);
end

end

    コード生成で使用する double の行列の型を作成するには、関数 coder.newtype を使用します。

    A = coder.newtype('int32', [1 30], [0 1]);
B = coder.newtype('int32', [1 1], [0 0]);
inputArgs = {A,B};

    CUDA ライブラリを生成するには、関数 codegen を使用します。

    cfg = coder.gpuConfig('lib');
cfg.GenerateReport = true;

codegen -config cfg -args inputArgs myAtomicSub -d myAtomicSub

    生成された CUDA コードには、atomicSub() CUDA API の呼び出しを使用する myAtomicSub_kernel1 カーネルが含まれます。

    //
// File: myAtomicSub.cu
//
...

static __global__ __launch_bounds__(1024, 1) void myAtomicSub_kernel1(
    const int32_T b, const int32_T i, int32_T a_data[])
{
  uint64_T loopEnd;
  uint64_T threadId;
...

  loopEnd = static_cast<uint64_T>(i - 1);
  for (uint64_T idx{threadId}; idx <= loopEnd; idx += threadStride) {
    int32_T b_i;
    b_i = static_cast<int32_T>(idx);
    atomicSub(&a_data[b_i], b);
  }
}
...

void myAtomicSub(int32_T a_data[], int32_T a_size[2], int32_T b)
{
  dim3 block;
  dim3 grid;
...

    cudaMemcpy(gpu_a_data, a_data, a_size[1] * sizeof(int32_T),
               cudaMemcpyHostToDevice);
    myAtomicSub_kernel1<<<grid, block>>>(b, i, gpu_a_data);
    cudaMemcpy(a_data, gpu_a_data, a_size[1] * sizeof(int32_T),
               cudaMemcpyDeviceToHost);
...

}
...

}

    入力引数

    すべて折りたたむ

    オペランド。スカラー、ベクトル、行列、または多次元配列として指定します。入力 A と入力 B は以下の要件を満たさなければなりません。

    • 同じデータ型。

    • 同じサイズまたは互換性のあるサイズ。たとえば、A が M 行 N 列の行列で、B がスカラーまたは 1 行 N 列の行ベクトル。

    データ型: int32 | uint32

    バージョン履歴

    R2021b で導入

    参考

    関数

    トピック