Forum Discussion

v-m's avatar
v-m
Icon for New Contributor rankNew Contributor
2 years ago

Memory attributes for device_global

I am migrating IP component from HLS to oneAPI. The component is basic exponential moving average filtering. Implementation has state, which is saved between invocation. In HLS this can be achieved ...
High-level Design Tools
BoonBengT_Altera's avatar
BoonBengT_Altera
Icon for Moderator rankModerator
2 years ago

Hi @v-m,

Noted on the intention, we are checking to confirm internally on the implementation if we can/should be done this way.

Will get back to you as soon as we have an updates.

Just to understand further, as mention you are not able to apply the memory attributes on device_global.

Is there any error or complain from the compiler that you are seeing?


Regards

BB


v-m's avatar
v-m
Icon for New Contributor rankNew Contributor
2 years ago

Hello

I've tried several things. I assumed those attributes must be applied to device_global declaration directly. Here is some tests:

// error: 'private_copies' attribute only applies to local non-const variables and non-static data members
[[intel::private_copies(2)]]
sycl::ext::oneapi::experimental::device_global<int, FPGAProperties> value;

// error: 'fpga_register' attribute only applies to constant variables, local variables, static variables, and non-static data members
[[intel::fpga_register]]
sycl::ext::oneapi::experimental::device_global<int, FPGAProperties> value;

// no errors, but based on report - attribute wasn't applied
[[intel::fpga_register]]
static sycl::ext::oneapi::experimental::device_global<int, FPGAProperties> value;