DPCT1027
目次
DPCT1027#
メッセージ#
<reason> により、<API name> 呼び出しは 0 に置き換えられました。
詳細な説明#
機能的に互換性のある SYCL* API 呼び出しが存在しないオリジナル・アプリケーションの API 呼び出しは、インテル® DPC++ 互換性ツールがこの呼び出しを削除してもプログラムロジックに影響しないと判断し、同時にその呼び出しの戻り値がエラー処理に使用される場合、0 に置き換えられます。
置き換えには次のような理由が考えられます:
SYCL* は現在、デバイスでリソース制限をサポートしていません。
SYCL* は現在、USM を特定のキューに関連付けることをサポートしていません。
SYCL* は現在、キューに対する照会操作をサポートしていません。
SYCL* は現在、キューに対するキャプチャー操作をサポートしていません。
SYCL* は現在、デバイス上での共有メモリーの設定をサポートしていません。
SYCL* は現在、デバイスでキャッシュの設定をサポートしていません。
SYCL* は現在、デバイスで使用する既存のホストメモリーの登録をサポートしていません。USM を使用して、ホストとデバイスが使用するメモリーを割り当てます。
SYCL* は現在、デバイス向けのフラグをサポートしていません。
SYCL* は現在、ピアデバイス間のメモリーアクセスをサポートしていません。
SYCL* には対応する API がありません。
SYCL* での呼び出しは冗長です。
修正方法の提案#
コードの正当性を検証してください。
例えば、以下のオリジナル CUDA* コードについて考えてみます。
1 __global__ void kernel() {
2 return;
3 }
4
5 void foo() {
6 int err = 0;
7 cudaLimit limit;
8 cudaStream_t stream;
9 unsigned int flags;
10 cudaSharedMemConfig config;
11
12 err = cudaDeviceSetLimit(limit, 0);
13 err = cudaStreamAttachMemAsync(stream, nullptr);
14 err = cudaStreamQuery(stream);
15 err = cudaStreamBeginCapture(stream, cudaStreamCaptureModeGlobal);
16 err = cudaDeviceSetSharedMemConfig(config);
17 err = cudaDeviceSetCacheConfig(cudaFuncCachePreferNone);
18 err = cuMemHostRegister(ptr, count, flags);
19 err = cudaSetDeviceFlags(flags);
20 err = cudaDeviceEnablePeerAccess(peer_device, flags);
21 err = cuInit(0);
22 float *aptr;
23 cudaStreamAttrValue stream_attribute = {};
24 stream_attribute.accessPolicyWindow.base_ptr = aptr;
25 stream_attribute.accessPolicyWindow.num_bytes = 8 * 8 * 8; 26 stream_attribute.accessPolicyWindow.hitRatio = 1.0f;
27 stream_attribute.accessPolicyWindow.hitProp = cudaAccessPropertyPersisting;
28 stream_attribute.accessPolicyWindow.missProp = cudaAccessPropertyStreaming;
29 err = cudaStreamSetAttribute(stream, cudaStreamAttributeAccessPolicyWindow, &stream_attribute);
30 err = cudaStreamGetAttribute(stream, cudaStreamAttributeAccessPolicyWindow, &stream_attribute);
31 err = cudaCtxResetPersistingL2Cache();
32 err = cuCtxResetPersistingL2Cache();
33 err = cudaFuncSetAttribute(kernel, cudaFuncAttributeMaxDynamicSharedMemorySize, 8 * 8 * 8);
34 }このコードは、以下の SYCL* コードに移行されます。
1 void kernel() {
2 return;
3 }
4
5 void foo() try {
6 int err = 0;
7 cudaLimit limit;
8 dpct::queue_ptr stream;
9 unsigned int flags;
10 int config;
11
12 /*
13 DPCT1027:0: The call to cudaDeviceSetLimit was replaced with 0 because SYCL
14 currently does not support setting resource limits on devices.
15 */
16 err = 0;
17 /*
18 DPCT1027:1: The call to cudaStreamAttachMemAsync was replaced with 0 because
19 SYCL currently does not support associating USM with a specific queue.
20 */
21 err = 0;
22 /*
23 DPCT1027:2: The call to cudaStreamQuery was replaced with 0 because SYCL
24 currently does not support query operations on queues.
25 */
26 err = 0;
27 /*
28 DPCT1027:3: The call to cudaDeviceSetSharedMemConfig was replaced with 0
29 because SYCL currently does not support configuring shared memory on devices.
30 */
31 err = 0;
32 /*
33 DPCT1027:4: The call to cudaDeviceSetCacheConfig was replaced with 0 because
34 SYCL currently does not support setting cache config on devices.
35 */
36 err = 0;
37 /*
38 DPCT1027:5: The call to cudaSetDeviceFlags was replaced with 0 because SYCL
39 currently does not support setting flags for devices.
40 */
41 err = 0;
42 /*
43 DPCT1027:6: The call to cuInit was replaced with 0 because this call is
44 redundant in SYCL.
45 */
46 err = 0;
47 float *aptr;
48 /*
49 DPCT1007:7: Migration of cudaStreamAttributeValue is not supported.
50 */
51 cudaStreamAttrValue stream_attribute = {};
52 /*
53 DPCT1027:8: The call to cudaStreamSetAttribute was removed because SYCL currently
54 does not support setting cache config on devices.
55 */
56 err = 0;
57 /*
58 DPCT1027:9: The call to cudaDeviceSetCacheConfig was removed because SYCL
59 currently does not support setting cache config on devices.
60 */
61 err = 0;
62 /*
63 DPCT1027:10: The call to cudaDeviceSetCacheConfig was removed because SYCL
64 currently does not support setting cache config on devices.
65 */
66 err = 0;
67 /*
68 DPCT1027:11: The call to cuCtxResetPersistingL2Cache was removed because SYCL
69 currently does not support setting cache config on devices.
70 */
71 err = 0;
72 /*
73 DPCT1027:12: The call to cudaStreamQuery was removed because SYCL currently
74 does not support query operations on queues.
75 */
76 err = 0;
77 /*
78 DPCT1027:13: The call to cudaStreamQuery was removed because SYCL currently
79 does not support query operations on queues.
80 */
81 err = 0;
82 }
83 catch (sycl::exception const &exc) {
84 std::cerr << exc.what() << "Exception caught at file:" << __FILE__
85 << ", line:" << __LINE__ << std::endl;
86 std::exit(1);
87 }このコードは次のように書き換えられます。
1 void foo() {
2 int err = 0;
3 cudaLimit limit;
4 dpct::queue_ptr stream;
5 unsigned int flags;
6 int config;
7 float *aptr;
8 }