Added C-API DPCTLQueue_HasEnableProfiling

This calls sycl::queue::has_property<sycl::property::queue::enable_profiling>()

Author: oleksandr-pavlyk

dpctl-capi/include/dpctl_sycl_queue_interface.h

@@ -333,6 +333,17 @@ void DPCTLQueue_MemAdvise(__dpctl_keep DPCTLSyclQueueRef QRef,
 DPCTL_API
 bool DPCTLQueue_IsInOrder(__dpctl_keep const DPCTLSyclQueueRef QRef);
 
+/*!
+ * @brief C-API wrapper for
+ * sycl::queue::has_property<sycl::property::queue::enable_profiling>() that
+ * indicates whether the referenced queue was constructed with this property.
+ *
+ * @param    QRef         An opaque pointer to the ``sycl::queue``.
+ * @ingroup QueueInterface
+ */
+DPCTL_API
+bool DPCTLQueue_HasEnableProfiling(__dpctl_keep const DPCTLSyclQueueRef QRef);
+
 /*!
  * @brief C-API wrapper for std::hash<sycl::queue>'s operator().
  *

dpctl-capi/source/dpctl_sycl_queue_interface.cpp

@@ -520,6 +520,16 @@ bool DPCTLQueue_IsInOrder(__dpctl_keep const DPCTLSyclQueueRef QRef)
         return false;
 }
 
+bool DPCTLQueue_HasEnableProfiling(__dpctl_keep const DPCTLSyclQueueRef QRef)
+{
+    auto Q = unwrap(QRef);
+    if (Q) {
+        return Q->has_property<sycl::property::queue::enable_profiling>();
+    }
+    else
+        return false;
+}
+
 size_t DPCTLQueue_Hash(__dpctl_keep const DPCTLSyclQueueRef QRef)
 {
     auto Q = unwrap(QRef);

dpctl-capi/tests/test_sycl_queue_interface.cpp

@@ -115,7 +115,7 @@ TEST(TestDPCTLSyclQueueInterface, CheckCopy)
     EXPECT_NO_FATAL_FAILURE(DPCTLDevice_Delete(DRef));
 }
 
-TEST(TestDPCTLSyclQueueInterface, CheckCopy_Invalid)
+TEST(TestDPCTLSyclQueueInterface, CheckCopyInvalid)
 {
     DPCTLSyclQueueRef Q1 = nullptr;
     DPCTLSyclQueueRef Q2 = nullptr;
@@ -125,7 +125,7 @@ TEST(TestDPCTLSyclQueueInterface, CheckCopy_Invalid)
     EXPECT_NO_FATAL_FAILURE(DPCTLQueue_Delete(Q2));
 }
 
-TEST(TestDPCTLSyclQueueInterface, CheckAreEq_False)
+TEST(TestDPCTLSyclQueueInterface, CheckAreEqFalse)
 {
     DPCTLSyclDeviceSelectorRef DSRef = nullptr;
     DPCTLSyclDeviceRef DRef = nullptr;
@@ -152,7 +152,7 @@ TEST(TestDPCTLSyclQueueInterface, CheckAreEq_False)
     EXPECT_NO_FATAL_FAILURE(DPCTLDeviceSelector_Delete(DSRef));
 }
 
-TEST(TestDPCTLSyclQueueInterface, CheckAreEq_True)
+TEST(TestDPCTLSyclQueueInterface, CheckAreEqTrue)
 {
     DPCTLSyclDeviceSelectorRef DSRef = nullptr;
     DPCTLSyclDeviceRef DRef = nullptr;
@@ -172,7 +172,7 @@ TEST(TestDPCTLSyclQueueInterface, CheckAreEq_True)
     EXPECT_NO_FATAL_FAILURE(DPCTLDeviceSelector_Delete(DSRef));
 }
 
-TEST(TestDPCTLSyclQueueInterface, CheckAreEq_Invalid)
+TEST(TestDPCTLSyclQueueInterface, CheckAreEqInvalid)
 {
     DPCTLSyclDeviceSelectorRef DSRef = nullptr;
     DPCTLSyclDeviceRef DRef = nullptr;
@@ -192,31 +192,31 @@ TEST(TestDPCTLSyclQueueInterface, CheckAreEq_Invalid)
     EXPECT_NO_FATAL_FAILURE(DPCTLDeviceSelector_Delete(DSRef));
 }
 
-TEST(TestDPCTLSyclQueueInterface, CheckHash_Invalid)
+TEST(TestDPCTLSyclQueueInterface, CheckHashInvalid)
 {
     DPCTLSyclQueueRef Q1 = nullptr;
     DPCTLSyclQueueRef Q2 = nullptr;
     EXPECT_TRUE(DPCTLQueue_Hash(Q1) == 0);
     EXPECT_TRUE(DPCTLQueue_Hash(Q2) == 0);
 }
 
-TEST(TestDPCTLSyclQueueInterface, CheckGetBackend_Invalid)
+TEST(TestDPCTLSyclQueueInterface, CheckGetBackendInvalid)
 {
     DPCTLSyclQueueRef Q = nullptr;
     DPCTLSyclBackendType Bty = DPCTL_UNKNOWN_BACKEND;
     EXPECT_NO_FATAL_FAILURE(Bty = DPCTLQueue_GetBackend(Q));
     EXPECT_TRUE(Bty == DPCTL_UNKNOWN_BACKEND);
 }
 
-TEST(TestDPCTLSyclQueueInterface, CheckGetContext_Invalid)
+TEST(TestDPCTLSyclQueueInterface, CheckGetContextInvalid)
 {
     DPCTLSyclQueueRef Q = nullptr;
     DPCTLSyclContextRef CRef = nullptr;
     EXPECT_NO_FATAL_FAILURE(CRef = DPCTLQueue_GetContext(Q));
     EXPECT_TRUE(CRef == nullptr);
 }
 
-TEST(TestDPCTLSyclQueueInterface, CheckGetDevice_Invalid)
+TEST(TestDPCTLSyclQueueInterface, CheckGetDeviceInvalid)
 {
     DPCTLSyclQueueRef Q = nullptr;
     DPCTLSyclDeviceRef DRef = nullptr;
@@ -250,14 +250,48 @@ TEST(TestDPCTLSyclQueueInterface, CheckIsInOrder)
     EXPECT_NO_FATAL_FAILURE(DPCTLDeviceSelector_Delete(DSRef));
 }
 
-TEST(TestDPCTLSyclQueueInterface, CheckIsInOrder_Invalid)
+TEST(TestDPCTLSyclQueueInterface, CheckIsInOrderInvalid)
 {
     bool ioq = true;
     DPCTLSyclQueueRef Q1 = nullptr;
     EXPECT_NO_FATAL_FAILURE(ioq = DPCTLQueue_IsInOrder(Q1));
     EXPECT_FALSE(ioq);
 }
 
+TEST(TestDPCTLSyclQueueInterface, CheckHasEnableProfiling)
+{
+    bool ioq = true;
+    DPCTLSyclDeviceSelectorRef DSRef = nullptr;
+    DPCTLSyclDeviceRef DRef = nullptr;
+    DPCTLSyclQueueRef Q1 = nullptr;
+    DPCTLSyclQueueRef Q2 = nullptr;
+
+    EXPECT_NO_FATAL_FAILURE(DSRef = DPCTLDefaultSelector_Create());
+    EXPECT_NO_FATAL_FAILURE(DRef = DPCTLDevice_CreateFromSelector(DSRef));
+    EXPECT_NO_FATAL_FAILURE(
+        Q1 = DPCTLQueue_CreateForDevice(DRef, nullptr, DPCTL_DEFAULT_PROPERTY));
+    EXPECT_NO_FATAL_FAILURE(ioq = DPCTLQueue_HasEnableProfiling(Q1));
+    EXPECT_FALSE(ioq);
+
+    EXPECT_NO_FATAL_FAILURE(
+        Q2 = DPCTLQueue_CreateForDevice(DRef, nullptr, DPCTL_ENABLE_PROFILING));
+    EXPECT_NO_FATAL_FAILURE(ioq = DPCTLQueue_HasEnableProfiling(Q2));
+    EXPECT_TRUE(ioq);
+
+    EXPECT_NO_FATAL_FAILURE(DPCTLQueue_Delete(Q1));
+    EXPECT_NO_FATAL_FAILURE(DPCTLQueue_Delete(Q2));
+    EXPECT_NO_FATAL_FAILURE(DPCTLDevice_Delete(DRef));
+    EXPECT_NO_FATAL_FAILURE(DPCTLDeviceSelector_Delete(DSRef));
+}
+
+TEST(TestDPCTLSyclQueueInterface, CheckHasEnableProfilingInvalid)
+{
+    bool ioq = true;
+    DPCTLSyclQueueRef Q1 = nullptr;
+    EXPECT_NO_FATAL_FAILURE(ioq = DPCTLQueue_HasEnableProfiling(Q1));
+    EXPECT_FALSE(ioq);
+}
+
 TEST_P(TestDPCTLQueueMemberFunctions, CheckGetBackend)
 {
     auto q = unwrap(QRef);