added DPCTLQueue_IsInOrder

Author: oleksandr-pavlyk

dpctl-capi/include/dpctl_sycl_queue_interface.h

@@ -312,4 +312,14 @@ void DPCTLQueue_MemAdvise(__dpctl_keep DPCTLSyclQueueRef QRef,
                           size_t Count,
                           int Advice);
 
+/*!
+ * @brief C-API wrapper for sycl::queue::is_in_order that indicates whether
+ * the referenced queue is in-order or out-of-order.
+ *
+ * @param    QRef         An opaque pointer to the sycl queue.
+ * @ingroup QueueInterface
+ */
+DPCTL_API
+bool DPCTLQueue_IsInOrder(__dpctl_keep const DPCTLSyclQueueRef QRef);
+
 DPCTL_C_EXTERN_C_END

dpctl-capi/source/dpctl_sycl_queue_interface.cpp

@@ -450,7 +450,8 @@ void DPCTLQueue_Wait(__dpctl_keep DPCTLSyclQueueRef QRef)
     // \todo what happens if the QRef is null or a pointer to a valid sycl
     // queue
     auto SyclQueue = unwrap(QRef);
-    SyclQueue->wait();
+    if (SyclQueue)
+        SyclQueue->wait();
 }
 
 void DPCTLQueue_Memcpy(__dpctl_keep const DPCTLSyclQueueRef QRef,
@@ -459,17 +460,21 @@ void DPCTLQueue_Memcpy(__dpctl_keep const DPCTLSyclQueueRef QRef,
                        size_t Count)
 {
     auto Q = unwrap(QRef);
-    auto event = Q->memcpy(Dest, Src, Count);
-    event.wait();
+    if (Q) {
+        auto event = Q->memcpy(Dest, Src, Count);
+        event.wait();
+    }
 }
 
 void DPCTLQueue_Prefetch(__dpctl_keep DPCTLSyclQueueRef QRef,
                          const void *Ptr,
                          size_t Count)
 {
     auto Q = unwrap(QRef);
-    auto event = Q->prefetch(Ptr, Count);
-    event.wait();
+    if (Q) {
+        auto event = Q->prefetch(Ptr, Count);
+        event.wait();
+    }
 }
 
 void DPCTLQueue_MemAdvise(__dpctl_keep DPCTLSyclQueueRef QRef,
@@ -478,6 +483,19 @@ void DPCTLQueue_MemAdvise(__dpctl_keep DPCTLSyclQueueRef QRef,
                           int Advice)
 {
     auto Q = unwrap(QRef);
-    auto event = Q->mem_advise(Ptr, Count, static_cast<pi_mem_advice>(Advice));
-    event.wait();
+    if (Q) {
+        auto event =
+            Q->mem_advise(Ptr, Count, static_cast<pi_mem_advice>(Advice));
+        event.wait();
+    }
+}
+
+bool DPCTLQueue_IsInOrder(__dpctl_keep const DPCTLSyclQueueRef QRef)
+{
+    auto Q = unwrap(QRef);
+    if (Q) {
+        return Q->is_in_order();
+    }
+    else
+        return false;
 }

dpctl-capi/tests/test_sycl_queue_interface.cpp

@@ -255,6 +255,22 @@ TEST_P(TestDPCTLQueueMemberFunctions, CheckGetDevice)
     DPCTLDevice_Delete(D);
 }
 
+TEST_P(TestDPCTLQueueMemberFunctions, CheckIsInOrder)
+{
+    bool ioq = true;
+
+    EXPECT_NO_FATAL_FAILURE(ioq = DPCTLQueue_IsInOrder(QRef));
+    EXPECT_FALSE(ioq);
+
+    DPCTLSyclQueueRef QRef_ioq = nullptr;
+    EXPECT_NO_FATAL_FAILURE(
+        QRef_ioq = DPCTLQueue_CreateForDevice(DRef, nullptr, DPCTL_IN_ORDER));
+    EXPECT_TRUE(QRef_ioq);
+    EXPECT_NO_FATAL_FAILURE(ioq = DPCTLQueue_IsInOrder(QRef_ioq));
+    EXPECT_TRUE(ioq);
+    EXPECT_NO_FATAL_FAILURE(DPCTLQueue_Delete(QRef_ioq));
+}
+
 INSTANTIATE_TEST_SUITE_P(DPCTLQueueMemberFuncTests,
                          TestDPCTLQueueMemberFunctions,
                          ::testing::Values("opencl:gpu:0",