インテル® グラフィックス・テクノロジー

インテル® グラフィックス・テクノロジー向けコンパイル

インテル® グラフィックス・テクノロジー向けのオフロード拡張を含むソースファイルをコンパイルする場合、生成されるオブジェクト・ファイルにターゲット・オブジェクトが組込まれます。このオブジェクト・ファイルは fat オブジェクトと呼ばれます。ターゲット・オブジェクトのセクション名は .gfxobj です。FAT オブジェクトをリンクする場合、ターゲット実行ファイルは次のようになります。

• .gfx bin (Windows*) という名前のセクションがホスト実行ファイルに組込まれます。

• __gfx_offload_target_image (Linux*) という名前のオブジェクトが読み取り専用データセクションに配置されます。

ターゲット・オブジェクトまたはターゲット実行ファイルは、offload_extract ツールを使用して FAT オブジェクトまたは FAT 実行ファイルから抽出できます。

インテル® グラフィックス・テクノロジー向けプログラミング

コンパイラーは、プロセッサー・グラフィックスへのオフロードで、次のプログラミング・モデルをサポートします。

• OpenMP* オフロードモデル: OpenMP* 仕様で定義されている多くのオフロード構造がサポートされます。利用可能なオフロード構造の一覧は、OpenMP* ベースのオフロードに関するセクションにあります。各オフロード構造の説明は、openmp.org (英語) を参照してください。

  コンパイラーは、「OpenMP* プラグマの概要」に記載されている OpenMP* オフロード構造の多くのをサポートします。各オフロード構造の詳細は、openmp.org (英語) にある OpenMP* 仕様を参照してください。

  要約すると、distribute 構造と parallel for 以外の並列構造を除く、OpenMP* オフロードプラグマの多くはサポートされます。例えば、nowait 節と depend 節を使用する非同期オフロードとタスクの依存性はサポートされます。

  プロセッサー・グラフィックス向けの OpenMP* ベースのオフロードを有効にするには、コンパイラーに次のオプションを渡します。

  -qopenmp -qopenmp-offload=gfx (Linux*)

  /Qopenmp /Qopenmp-offload=gfx (Windows*)

• インテル® Cilk™ Plus 言語拡張のサブセット: コンパイラーは、オフロードコードとスレッドグループのローカルデータで、_Cilk_for、_Thread_group、__thread_group_local キーワードによる並列処理の指定をサポートします。また、#pragma offload 構文によるオフロードの指定もサポートします。

  インテル® Cilk™ Plus は、インテル® C++ コンパイラー 18.0 では非推奨の古い機能です。プロセッサー・グラフィックスへオフロードする代替手段は、将来のリリースで提供される予定です。詳細は、「インテル® Cilk™ Plus の代わりに OpenMP* またはインテル® TBB を使用するためのアプリケーションの移行」を参照してください。

• API ベースのオフロード: このモデルでは、オフロードするために #pragma offload や #pragma omp target のような特別な構文は使用しません。代わりに、インテル® グラフィックス・テクノロジーのオフロードランタイムで実装されている API 関数を使用して、データ設定とオフロードを表現します。

プログラミング・モデルが同期オフロード、非同期オフロード、または両方をサポートするかどうかは重要です。同期オフロードでは、オフロードを開始する CPU スレッドは常にオフロードが完了するまで待機します。オフロード処理は、データの共有/非共有を伴います。多くの場合、同期オフロードは非効率的です。例えば、オフロードを開始した CPU スレッドは、オフロードが完了するまで待機する代わりに有用な作業を行うことができます。また、1 回共有することで、同じデータを複数のオフロードで使用できることもあります。そのような場合は、非同期オフロードを使用すべきです。3 つのプログラミング・モデルのうち、OpenMP* ベースのモデルとインテル® Cilk™ Plus ベースのモデルは同期モードと非同期モードをサポートしますが、API ベースのモデルは非同期モードのみサポートします。

コンパイラーは、インテル® グラフィックス・テクノロジー・向けのプログラミングを支援するため、次の言語拡張を提供しています。

• offload プラグマと offload_attribute プラグマ。並列領域は _Cilk_for ループまたは配列表記文で表現。

• インテル® グラフィックス・テクノロジー向けのプログラミングで利用できる事前定義済みマクロ。

• 変数と関数をターゲット上に配置する属性。

• インテル® グラフィックス・テクノロジー向けヘテロジニアス・プログラミング用のビルトイン関数および多数の既存の CPU 用の組込み関数。

• 同期/非同期オフロード API は、カーネル関数のオフロードキューの管理と CPU とプロセッサー・グラフィックス間のデータ共有を容易にします。

CPU とプロセッサーグラフィック間でメモリーを共有するモードは 2 つあります。

• デフォルトのプログラミング・モデル: CPU とプロセッサー・グラフィック間で物理メモリーを共有できます。仮想メモリーは共有できません。

• 共有仮想メモリー (SVM): CPU とプロセッサー・ブラフィックス間で仮想アドレス空間を共有できます。

共有仮想メモリーに関するセクションに、SVM モードを使用する場合のプログラミングの相違点の説明があります。

インテル® グラフィックス・テクノロジー向けビルド

コンパイラーには、インテル® グラフィックス・テクノロジー用のバイナリーをビルドする際に使用できる、次のコンパイラー・オプションと環境変数が用意されています。

インテル® グラフィックス・テクノロジーで利用可能な環境変数の一部を以下に示します。