diff --git a/sycl/plugins/hip/pi_hip.cpp b/sycl/plugins/hip/pi_hip.cpp index 01d76ac0702e3..c0578f6b9a8ad 100644 --- a/sycl/plugins/hip/pi_hip.cpp +++ b/sycl/plugins/hip/pi_hip.cpp @@ -1767,8 +1767,17 @@ pi_result hip_piDeviceGetInfo(pi_device device, pi_device_info param_name, return getInfo(param_value_size, param_value, param_value_size_ret, value); } + case PI_DEVICE_INFO_ATOMIC_64: { + // TODO: Reconsider it when AMD supports SYCL_USE_NATIVE_FP_ATOMICS. + hipDeviceProp_t props; + cl::sycl::detail::pi::assertion( + hipGetDeviceProperties(&props, device->get()) == hipSuccess); + return getInfo(param_value_size, param_value, param_value_size_ret, + props.arch.hasGlobalInt64Atomics && + props.arch.hasSharedInt64Atomics); + } + // TODO: Implement. - case PI_DEVICE_INFO_ATOMIC_64: case PI_DEVICE_INFO_ATOMIC_MEMORY_ORDER_CAPABILITIES: // TODO: Investigate if this information is available on HIP. case PI_DEVICE_INFO_ATOMIC_MEMORY_SCOPE_CAPABILITIES: