From c213da660ac33ba4b6d780a679cfa883c4ad5002 Mon Sep 17 00:00:00 2001 From: pgorlani Date: Fri, 8 Jul 2022 10:16:47 -0400 Subject: [PATCH] [SYCL][HIP] Implement PI_DEVICE_INFO_ATOMIC_64 --- sycl/plugins/hip/pi_hip.cpp | 11 ++++++++++- 1 file changed, 10 insertions(+), 1 deletion(-) 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: