diff --git a/sycl/plugins/cuda/pi_cuda.cpp b/sycl/plugins/cuda/pi_cuda.cpp index a5f8f2faacd4a..ba7e57ee7fbf3 100644 --- a/sycl/plugins/cuda/pi_cuda.cpp +++ b/sycl/plugins/cuda/pi_cuda.cpp @@ -1283,7 +1283,7 @@ pi_result cuda_piDeviceGetInfo(pi_device device, pi_device_info param_name, device->get()) == CUDA_SUCCESS); cl::sycl::detail::pi::assertion((ecc_enabled == 0) | (ecc_enabled == 1)); - auto result = static_cast(ecc_enabled); + auto result = static_cast(ecc_enabled); return getInfo(param_value_size, param_value, param_value_size_ret, result); } case PI_DEVICE_INFO_HOST_UNIFIED_MEMORY: { @@ -1294,7 +1294,7 @@ pi_result cuda_piDeviceGetInfo(pi_device device, pi_device_info param_name, cl::sycl::detail::pi::assertion((is_integrated == 0) | (is_integrated == 1)); - auto result = static_cast(is_integrated); + auto result = static_cast(is_integrated); return getInfo(param_value_size, param_value, param_value_size_ret, result); } case PI_DEVICE_INFO_PROFILING_TIMER_RESOLUTION: { @@ -1304,16 +1304,20 @@ pi_result cuda_piDeviceGetInfo(pi_device device, pi_device_info param_name, size_t{1000u}); } case PI_DEVICE_INFO_ENDIAN_LITTLE: { - return getInfo(param_value_size, param_value, param_value_size_ret, true); + return getInfo(param_value_size, param_value, param_value_size_ret, + PI_TRUE); } case PI_DEVICE_INFO_AVAILABLE: { - return getInfo(param_value_size, param_value, param_value_size_ret, true); + return getInfo(param_value_size, param_value, param_value_size_ret, + PI_TRUE); } case PI_DEVICE_INFO_COMPILER_AVAILABLE: { - return getInfo(param_value_size, param_value, param_value_size_ret, true); + return getInfo(param_value_size, param_value, param_value_size_ret, + PI_TRUE); } case PI_DEVICE_INFO_LINKER_AVAILABLE: { - return getInfo(param_value_size, param_value, param_value_size_ret, true); + return getInfo(param_value_size, param_value, param_value_size_ret, + PI_TRUE); } case PI_DEVICE_INFO_EXECUTION_CAPABILITIES: { auto capability = CL_EXEC_KERNEL; @@ -1403,7 +1407,8 @@ pi_result cuda_piDeviceGetInfo(pi_device device, pi_device_info param_name, size_t{1024u}); } case PI_DEVICE_INFO_PREFERRED_INTEROP_USER_SYNC: { - return getInfo(param_value_size, param_value, param_value_size_ret, true); + return getInfo(param_value_size, param_value, param_value_size_ret, + PI_TRUE); } case PI_DEVICE_INFO_PARENT_DEVICE: { return getInfo(param_value_size, param_value, param_value_size_ret, diff --git a/sycl/plugins/rocm/pi_rocm.cpp b/sycl/plugins/rocm/pi_rocm.cpp index 687bd2ed935d8..3fbe384b22ad2 100644 --- a/sycl/plugins/rocm/pi_rocm.cpp +++ b/sycl/plugins/rocm/pi_rocm.cpp @@ -1233,7 +1233,7 @@ pi_result rocm_piDeviceGetInfo(pi_device device, pi_device_info param_name, device->get()) == hipSuccess); cl::sycl::detail::pi::assertion((ecc_enabled == 0) | (ecc_enabled == 1)); - auto result = static_cast(ecc_enabled); + auto result = static_cast(ecc_enabled); return getInfo(param_value_size, param_value, param_value_size_ret, result); } case PI_DEVICE_INFO_HOST_UNIFIED_MEMORY: { @@ -1244,7 +1244,7 @@ pi_result rocm_piDeviceGetInfo(pi_device device, pi_device_info param_name, cl::sycl::detail::pi::assertion((is_integrated == 0) | (is_integrated == 1)); - auto result = static_cast(is_integrated); + auto result = static_cast(is_integrated); return getInfo(param_value_size, param_value, param_value_size_ret, result); } case PI_DEVICE_INFO_PROFILING_TIMER_RESOLUTION: { @@ -1254,16 +1254,20 @@ pi_result rocm_piDeviceGetInfo(pi_device device, pi_device_info param_name, size_t{1000u}); } case PI_DEVICE_INFO_ENDIAN_LITTLE: { - return getInfo(param_value_size, param_value, param_value_size_ret, true); + return getInfo(param_value_size, param_value, param_value_size_ret, + PI_TRUE); } case PI_DEVICE_INFO_AVAILABLE: { - return getInfo(param_value_size, param_value, param_value_size_ret, true); + return getInfo(param_value_size, param_value, param_value_size_ret, + PI_TRUE); } case PI_DEVICE_INFO_COMPILER_AVAILABLE: { - return getInfo(param_value_size, param_value, param_value_size_ret, true); + return getInfo(param_value_size, param_value, param_value_size_ret, + PI_TRUE); } case PI_DEVICE_INFO_LINKER_AVAILABLE: { - return getInfo(param_value_size, param_value, param_value_size_ret, true); + return getInfo(param_value_size, param_value, param_value_size_ret, + PI_TRUE); } case PI_DEVICE_INFO_EXECUTION_CAPABILITIES: { auto capability = CL_EXEC_KERNEL; @@ -1333,7 +1337,8 @@ pi_result rocm_piDeviceGetInfo(pi_device device, pi_device_info param_name, size_t{1024u}); } case PI_DEVICE_INFO_PREFERRED_INTEROP_USER_SYNC: { - return getInfo(param_value_size, param_value, param_value_size_ret, true); + return getInfo(param_value_size, param_value, param_value_size_ret, + PI_TRUE); } case PI_DEVICE_INFO_PARENT_DEVICE: { return getInfo(param_value_size, param_value, param_value_size_ret,