DPCT1127

Intel® DPC++ Compatibility Tool Developer Guide and Reference

Download PDF

ID 768918

Date 6/24/2024

Version

Public

A newer version of this document is available. Customers should click here to go to the newest version.

Visible to Intel only — GUID: GUID-FFDC2583-BF68-4A78-8DA9-23F42E200B96

View Details

DPCT1127

Message

The constant compile-time initialization for device_global is supported when compiling with C++20. You may need to adjust the compile commands.

Detailed Help

The device_global extension introduces device scoped memory allocations into SYCL* that can be accessed within a kernel, using syntax similar to C++ global variables. Constant compile-time initialization for device_global is supported when compiling with C++20. Ref: https://github.com/intel/llvm/blob/sycl/sycl/doc/extensions/experimental/sycl_ext_oneapi_device_global.asciidoc.

Suggestions to Fix

For example, this original CUDA* code:

// test.cu
__constant__ int var = 0;
__global__ void kernel(int* ptr) {
  *ptr = var;
}

results in the following migrated SYCL code:

// test.dp.cpp
/*
DPCT1127:0: The constant compile-time initialization for device_global is
supported when compiling with C++20. You may need to adjust the compile
commands.
*/
static sycl::ext::oneapi::experimental::device_global<const int> var{0};
void kernel(int* ptr) {
  *ptr = var.get();
}

The compile commands need to be rewritten to:

icpx -fsycl -std=c++20 test.dp.cpp # Linux
icx-cl -fsycl -Qstd=c++20 test.dp.cpp # Windows

Select Your Language

Using Intel.com Search

Quick Links

Recent Searches

Advanced Search

Only search in

Intel® DPC++ Compatibility Tool Developer Guide and Reference

DPCT1127

Message

Detailed Help

Suggestions to Fix