DPCT1026#

メッセージ#

<reason> により、<API name> 呼び出しは削除されました。

説明#

機能的に互換性のある SYCL* API 呼び出しが存在しないオリジナル・アプリケーションの API 呼び出しは、インテル® DPC++ 互換性ツールがプログラムロジックに影響を与えないと判断した場合削除されます。

削除には次のような理由が考えられます:

  • SYCL* は現在、デバイスでリソース制限をサポートしていません。

  • SYCL* は現在、USM を特定のキューに関連付けることをサポートしていません。

  • SYCL* は現在、キューに対する照会操作をサポートしていません。

  • SYCL* は現在、キューに対するキャプチャー操作をサポートしていません。

  • SYCL* は現在、デバイス上での共有メモリーの設定をサポートしていません。

  • SYCL* は現在、デバイスでキャッシュの設定をサポートしていません。

  • SYCL* は現在、デバイスで使用する既存のホストメモリーの登録をサポートしていません。USM を使用して、ホストとデバイスが使用するメモリーを割り当てます。

  • SYCL* は現在、デバイス向けのフラグをサポートしていません。

  • SYCL* は現在、ピアデバイス間のメモリーアクセスをサポートしていません。

  • SYCL* には対応する API がありません。

  • SYCL* での呼び出しは冗長です。

修正方法の提案#

コードの正当性を検証してください。

例えば、以下のオリジナル CUDA* コードについて考えてみます。

1__device__ void bar(int *a) { 
2 __ldg(a); 
3} 
4 
5void foo() { 
6 cudaLimit limit; 
7 cudaStream_t stream; 
8 unsigned int flags; 
9 cudaSharedMemConfig config; 
10 
11 cudaDeviceSetLimit(limit, 0); 
12 cudaStreamAttachMemAsync(stream, nullptr); 
13 cudaStreamQuery(stream); 
14 cudaDeviceSetSharedMemConfig(config); 
15 cudaDeviceSetCacheConfig(cudaFuncCachePreferNone); 
16 cudaSetDeviceFlags(flags); 
17 cuInit(0); 
18}

このコードは、以下の SYCL* コードに移行されます。

1void bar(int *a) { 
2 /* 
3 DPCT1026:0: The call to __ldg was removed because there is no corresponding 
4 API in SYCL.5 */ 
6 *a; 
7} 
8 
9void foo() { 
10 cudaLimit limit; 
11 dpct::queue_ptr stream; 
12 unsigned int flags; 
13 int config; 
14 
15 /* 
16 DPCT1026:1: The call to cudaDeviceSetLimit was removed because SYCL currently 
17 does not support setting resource limits on devices.18 */ 
19 /* 
20 DPCT1026:2: The call to cudaStreamAttachMemAsync was removed because SYCL 
21 currently does not support associating USM with a specific queue.22 */ 
23 /* 
24 DPCT1026:3: The call to cudaStreamQuery was removed because SYCL currently 
25 does not support query operations on queues.26 */ 
27 /* 
28 DPCT1026:4: The call to cudaDeviceSetSharedMemConfig was removed because SYCL 
29 currently does not support configuring shared memory on devices.30 */ 
31 /* 
32 DPCT1026:5: The call to cudaDeviceSetCacheConfig was removed because SYCL 
33 currently does not support setting cache config on devices.34 */ 
35 /* 
36 DPCT1026:6: The call to cudaSetDeviceFlags was removed because SYCL currently 
37 does not support setting flags for devices.38 */ 
39 /* 
40 DPCT1026:7: The call to cuInit was removed because this call is redundant in 
41 SYCL.42 */ 
43}

このコードは次のように書き換えられます。

1void bar(int *a) { 
2 *a; 
3} 
4 
5void foo() { 
6 cudaLimit limit; 
7 dpct::queue_ptr stream; 
8 unsigned int flags; 
9 size_t count; 
10 float *ptr; 
11 
12 int config; 
13}