CUDAスレッド同期
をテンプレートにして作成
[
トップ
|
新規
|
一覧
|
検索
|
最終更新
|
ヘルプ
]
開始行:
*CUDAスレッドについて [#z58df11d]
カーネル呼び出し(<<< >>>)で複数のスレッドを同時に立ち上げ...
これらのスレッドは同時には実行されません．スレッドの呼び...
必要なので，例えば，100スレッドを一斉に動かすと，最初と最...
100クロックずれます．
このような''非同期''のスレッドを同期させるのが''__syncthr...
また，メモリアクセスに対する排他制御を行うのが''__threadf...
**__syncthreads() [#cc24078e]
[[CUDAで行列演算：乗算(シェアードメモリ使用版)]]でも説明...
カーネル関数中に''__syncthreads()''を記述すると，
その行が同期点として設定されます．
各スレッドは処理が同期点に達すると，他のスレッドがその同...
同期点がバリアのような働きをするのでバリア同期と呼ばれま...
注意点として，''__syncthreads()''によるバリアは同一ブロッ...
これは，性能の異なる複数の異なるデバイスを組み合わせて実...
処理の速いデバイスが処理の遅いデバイスに合わせられ，
全体のパフォーマンスが低下することを防ぐためです．
異なるブロックの同期(グローバル同期)が必要な場合は，一度...
**__threadfence()，__threadfence_block() [#gf05edfa]
void __threadfence();
は__threadfence()より前に呼ばれたスレッドによるメモリアク...
デバイス内(シェアードメモリの場合はブロック内)の全てのス...
データの書き込み中に他のスレッドからのアクセスを防いでく...
__threadfence_block()はブロック内の全スレッドが対象です．
終了行:
*CUDAスレッドについて [#z58df11d]
カーネル呼び出し(<<< >>>)で複数のスレッドを同時に立ち上げ...
これらのスレッドは同時には実行されません．スレッドの呼び...
必要なので，例えば，100スレッドを一斉に動かすと，最初と最...
100クロックずれます．
このような''非同期''のスレッドを同期させるのが''__syncthr...
また，メモリアクセスに対する排他制御を行うのが''__threadf...
**__syncthreads() [#cc24078e]
[[CUDAで行列演算：乗算(シェアードメモリ使用版)]]でも説明...
カーネル関数中に''__syncthreads()''を記述すると，
その行が同期点として設定されます．
各スレッドは処理が同期点に達すると，他のスレッドがその同...
同期点がバリアのような働きをするのでバリア同期と呼ばれま...
注意点として，''__syncthreads()''によるバリアは同一ブロッ...
これは，性能の異なる複数の異なるデバイスを組み合わせて実...
処理の速いデバイスが処理の遅いデバイスに合わせられ，
全体のパフォーマンスが低下することを防ぐためです．
異なるブロックの同期(グローバル同期)が必要な場合は，一度...
**__threadfence()，__threadfence_block() [#gf05edfa]
void __threadfence();
は__threadfence()より前に呼ばれたスレッドによるメモリアク...
デバイス内(シェアードメモリの場合はブロック内)の全てのス...
データの書き込み中に他のスレッドからのアクセスを防いでく...
__threadfence_block()はブロック内の全スレッドが対象です．
ページ名:
![[PukiWiki]](image/pukiwiki.png "[PukiWiki]")
