stream logic

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;
 }

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<hipStream_t>(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) {