OpenACC Library相互運用性：デバイスポインタを取得する方法は？

Question

私たちはFortranで書かれたプロジェクトを持っています。

今私は、これはPGIコンパイラを使用して行うことができますが、私はライセンスが立ち往生する必要はありません知っています。

私たちは私たちのプロジェクトでOpenACCを使用できるかどうかを確認しようとしています。ここではgcc5.2のインストール手順を説明します。

https://github.com/olcf/OLCFHack15

今私はここに記載されているものと同様の何かをしたいです。具体的にはセクション8.3に記載されているものを

https://gcc.gnu.org/onlinedocs/libgomp/OpenACC-Library-Interoperability.html

。私はgfortranを使って正確に再現しようとしています。残念ながら、私はfortranでそれをどうやってやれるのか分かりません。例では、

d_X = acc_copyin(&h_X[0], N * sizeof (float)); 

これはD_Xが直接

s = cublasSaxpy(h, N, &alpha, d_X, 1, d_Y, 1); 

で使用することができます。しかし、FORTRANで、acc_copyinは何も返しません。

したがって、私はFortranでこのケースをどのように複製しますか？

Answer 1

あなたはcuBLASとのインターフェースを探していますか、これはもっと一般的ですか？ OpenACCソリューションは、通常は "data"ディレクティブを使用してデータを管理しますが、 "host_data"領域内からCUDA Cルーチンを呼び出します。 "host_data"は、デバイスポインタがこの領域で使用されるべきであることを指定します。そのため、cublasSaxpyに「d_X」を渡すと、デバイスポインタが渡されます。

cuBLASの注意事項では、上記のF77インターフェイスがホスト配列を予期しており、データの動きを管理します。したがって、正しいデバイスルーチンを呼び出すCUDA Cラッパー関数を記述する必要があります。 （CUDA Fortranはこのためのcublasモジュールを提供していますが、PGIのみです）

GNU 5.2は "host_data"をサポートしていませんが、ステータスページ（https://gcc.gnu.org/wiki/OpenACC）を見ていますFortran 6.0でもサポートされています。これは "host_data"が最適なソリューションであることから不幸です。

NVIDIAは、OpenACCツールキット（参照：https://developer.nvidia.com/openacc）の一部として、教育目的で学生や学者に無料のPGIライセンスを提供しています。