diff --git a/src/common/device_helpers.hip.h b/src/common/device_helpers.hip.h index 8003cca7f..05cc09c72 100644 --- a/src/common/device_helpers.hip.h +++ b/src/common/device_helpers.hip.h @@ -979,11 +979,6 @@ auto Reduce(Policy policy, InputIt first, InputIt second, Init init, Func reduce } catch (const std::exception& e) { throw; } - - // Check for any HIP errors after the reduction - hipError_t hip_err = hipGetLastError(); - if (hip_err != hipSuccess) { - } } return aggregate; } diff --git a/src/data/array_interface.cu b/src/data/array_interface.cu index 2058a72fd..8ce6bebb2 100644 --- a/src/data/array_interface.cu +++ b/src/data/array_interface.cu @@ -11,33 +11,6 @@ namespace xgboost { void ArrayInterfaceHandler::SyncCudaStream(std::int64_t stream) { -#if defined(XGBOOST_USE_HIP) - if (stream == 1 || stream == 2) { - // Default streams, no synchronization needed - return; - } - - hipEvent_t event; - hipError_t err = hipEventCreate(&event); - if (err != hipSuccess) { - LOG(WARNING) << "Failed to create HIP event: " << hipGetErrorString(err); - return; - } - - err = hipEventRecord(event, reinterpret_cast(stream)); - if (err != hipSuccess) { - LOG(WARNING) << "Failed to record HIP event: " << hipGetErrorString(err); - hipEventDestroy(event); - return; - } - - err = hipStreamWaitEvent(hipStreamPerThread, event, 0); - if (err != hipSuccess) { - LOG(WARNING) << "Failed to wait for HIP event: " << hipGetErrorString(err); - } - - hipEventDestroy(event); -#else switch (stream) { case 0: /** @@ -58,7 +31,6 @@ void ArrayInterfaceHandler::SyncCudaStream(std::int64_t stream) { dh::DefaultStream().Wait(e); } } -#endif } bool ArrayInterfaceHandler::IsCudaPtr(void const* ptr) {