From 7344ec4764e1842947a477630de7011773201404 Mon Sep 17 00:00:00 2001
From: "Kenneth Benzie (Benie)" <k.benzie83@gmail.com>
Date: Fri, 5 Jan 2024 15:58:59 +0000
Subject: [PATCH] Revert "[HIP] Implement ext_oneapi_queue_priority"

---
 source/adapters/hip/queue.cpp | 24 +++++-------------------
 source/adapters/hip/queue.hpp |  5 ++---
 2 files changed, 7 insertions(+), 22 deletions(-)

diff --git a/source/adapters/hip/queue.cpp b/source/adapters/hip/queue.cpp
index bf4b636c38..f01fc0e180 100644
--- a/source/adapters/hip/queue.cpp
+++ b/source/adapters/hip/queue.cpp
@@ -38,8 +38,8 @@ hipStream_t ur_queue_handle_t_::getNextComputeStream(uint32_t *StreamToken) {
       // The second check is done after mutex is locked so other threads can not
       // change NumComputeStreams after that
       if (NumComputeStreams < ComputeStreams.size()) {
-        UR_CHECK_ERROR(hipStreamCreateWithPriority(
-            &ComputeStreams[NumComputeStreams++], Flags, Priority));
+        UR_CHECK_ERROR(hipStreamCreateWithFlags(
+            &ComputeStreams[NumComputeStreams++], Flags));
       }
     }
     Token = ComputeStreamIdx++;
@@ -97,8 +97,8 @@ hipStream_t ur_queue_handle_t_::getNextTransferStream() {
     // The second check is done after mutex is locked so other threads can not
     // change NumTransferStreams after that
     if (NumTransferStreams < TransferStreams.size()) {
-      UR_CHECK_ERROR(hipStreamCreateWithPriority(
-          &TransferStreams[NumTransferStreams++], Flags, Priority));
+      UR_CHECK_ERROR(hipStreamCreateWithFlags(
+          &TransferStreams[NumTransferStreams++], Flags));
     }
   }
   uint32_t Stream_i = TransferStreamIdx++ % TransferStreams.size();
@@ -118,19 +118,6 @@ urQueueCreate(ur_context_handle_t hContext, ur_device_handle_t hDevice,
     std::unique_ptr<ur_queue_handle_t_> QueueImpl{nullptr};
 
     unsigned int Flags = 0;
-    ur_queue_flags_t URFlags = 0;
-    int Priority = 0; // Not guaranteed, but, in ROCm 5.7, 0 is the default
-
-    if (pProps && pProps->stype == UR_STRUCTURE_TYPE_QUEUE_PROPERTIES) {
-      URFlags = pProps->flags;
-      if (URFlags & UR_QUEUE_FLAG_PRIORITY_HIGH) {
-        ScopedContext Active(hContext->getDevice());
-        UR_CHECK_ERROR(hipDeviceGetStreamPriorityRange(nullptr, &Priority));
-      } else if (URFlags & UR_QUEUE_FLAG_PRIORITY_LOW) {
-        ScopedContext Active(hContext->getDevice());
-        UR_CHECK_ERROR(hipDeviceGetStreamPriorityRange(&Priority, nullptr));
-      }
-    }
 
     const bool IsOutOfOrder =
         pProps ? pProps->flags & UR_QUEUE_FLAG_OUT_OF_ORDER_EXEC_MODE_ENABLE
@@ -143,7 +130,7 @@ urQueueCreate(ur_context_handle_t hContext, ur_device_handle_t hDevice,
 
     QueueImpl = std::unique_ptr<ur_queue_handle_t_>(new ur_queue_handle_t_{
         std::move(ComputeHipStreams), std::move(TransferHipStreams), hContext,
-        hDevice, Flags, pProps ? pProps->flags : 0, Priority});
+        hDevice, Flags, pProps ? pProps->flags : 0});
 
     *phQueue = QueueImpl.release();
 
@@ -306,7 +293,6 @@ UR_APIEXPORT ur_result_t UR_APICALL urQueueCreateWithNativeHandle(
                              hDevice,
                              HIPFlags,
                              Flags,
-                             /*priority*/ 0,
                              /*backend_owns*/ pProperties->isNativeHandleOwned};
   (*phQueue)->NumComputeStreams = 1;
 
diff --git a/source/adapters/hip/queue.hpp b/source/adapters/hip/queue.hpp
index ad2f0f016e..c79bd293a3 100644
--- a/source/adapters/hip/queue.hpp
+++ b/source/adapters/hip/queue.hpp
@@ -44,7 +44,6 @@ struct ur_queue_handle_t_ {
   unsigned int LastSyncTransferStreams;
   unsigned int Flags;
   ur_queue_flags_t URFlags;
-  int Priority;
   // When ComputeStreamSyncMutex and ComputeStreamMutex both need to be
   // locked at the same time, ComputeStreamSyncMutex should be locked first
   // to avoid deadlocks
@@ -57,7 +56,7 @@ struct ur_queue_handle_t_ {
   ur_queue_handle_t_(std::vector<native_type> &&ComputeStreams,
                      std::vector<native_type> &&TransferStreams,
                      ur_context_handle_t Context, ur_device_handle_t Device,
-                     unsigned int Flags, ur_queue_flags_t URFlags, int Priority,
+                     unsigned int Flags, ur_queue_flags_t URFlags,
                      bool BackendOwns = true)
       : ComputeStreams{std::move(ComputeStreams)}, TransferStreams{std::move(
                                                        TransferStreams)},
@@ -67,7 +66,7 @@ struct ur_queue_handle_t_ {
         Device{Device}, RefCount{1}, EventCount{0}, ComputeStreamIdx{0},
         TransferStreamIdx{0}, NumComputeStreams{0}, NumTransferStreams{0},
         LastSyncComputeStreams{0}, LastSyncTransferStreams{0}, Flags(Flags),
-        URFlags(URFlags), Priority(Priority), HasOwnership{BackendOwns} {
+        URFlags(URFlags), HasOwnership{BackendOwns} {
     urContextRetain(Context);
     urDeviceRetain(Device);
   }