Added DPCTLPlatform_GetDefaultContext and tests

Author: oleksandr-pavlyk

libsyclinterface/include/dpctl_sycl_platform_interface.h

@@ -142,4 +142,16 @@ DPCTLPlatform_GetVersion(__dpctl_keep const DPCTLSyclPlatformRef PRef);
 DPCTL_API
 __dpctl_give DPCTLPlatformVectorRef DPCTLPlatform_GetPlatforms(void);
 
+/*!
+ * @brief  Returns a DPCTLSyclContextRef for default platform context.
+ *
+ * @param    PRef           Opaque pointer to a sycl::platform
+ * @return   A DPCTLSyclContextRef value for the default platform associated
+ * with this platform.
+ * @ingroup PlatformInterface
+ */
+DPCTL_API
+__dpctl_give DPCTLSyclContextRef
+DPCTLPlatform_GetDefaultContext(__dpctl_keep const DPCTLSyclPlatformRef PRef);
+
 DPCTL_C_EXTERN_C_END

libsyclinterface/source/dpctl_sycl_platform_interface.cpp

@@ -41,6 +41,7 @@ using namespace cl::sycl;
 namespace
 {
 DEFINE_SIMPLE_CONVERSION_FUNCTIONS(platform, DPCTLSyclPlatformRef);
+DEFINE_SIMPLE_CONVERSION_FUNCTIONS(context, DPCTLSyclContextRef);
 DEFINE_SIMPLE_CONVERSION_FUNCTIONS(device_selector, DPCTLSyclDeviceSelectorRef);
 DEFINE_SIMPLE_CONVERSION_FUNCTIONS(std::vector<DPCTLSyclPlatformRef>,
                                    DPCTLPlatformVectorRef);
@@ -202,3 +203,23 @@ __dpctl_give DPCTLPlatformVectorRef DPCTLPlatform_GetPlatforms()
     // the wrap function is defined inside dpctl_vector_templ.cpp
     return wrap(Platforms);
 }
+
+__dpctl_give DPCTLSyclContextRef
+DPCTLPlatform_GetDefaultContext(__dpctl_keep const DPCTLSyclPlatformRef PRef)
+{
+    auto P = unwrap(PRef);
+    if (P) {
+        try {
+            auto default_ctx = P->ext_oneapi_get_default_context();
+            return wrap(new context(default_ctx));
+        } catch (std::exception const &e) {
+            error_handler(e, __FILE__, __func__, __LINE__);
+            return nullptr;
+        }
+    }
+    else {
+        error_handler("Driver version cannot be looked up for a NULL platform.",
+                      __FILE__, __func__, __LINE__);
+        return nullptr;
+    }
+}

libsyclinterface/tests/test_sycl_platform_interface.cpp

@@ -25,6 +25,7 @@
 //===----------------------------------------------------------------------===//
 
 #include "Support/CBindingWrapping.h"
+#include "dpctl_sycl_context_interface.h"
 #include "dpctl_sycl_device_selector_interface.h"
 #include "dpctl_sycl_platform_interface.h"
 #include "dpctl_sycl_platform_manager.h"
@@ -82,6 +83,16 @@ void check_platform_backend(__dpctl_keep const DPCTLSyclPlatformRef PRef)
     }());
 }
 
+void check_platform_default_context(
+    __dpctl_keep const DPCTLSyclPlatformRef PRef)
+{
+    DPCTLSyclContextRef CRef = nullptr;
+    EXPECT_NO_FATAL_FAILURE(CRef = DPCTLPlatform_GetDefaultContext(PRef));
+    EXPECT_TRUE(CRef != nullptr);
+
+    EXPECT_NO_FATAL_FAILURE(DPCTLContext_Delete(CRef));
+}
+
 } // namespace
 
 struct TestDPCTLSyclPlatformInterface
@@ -207,6 +218,11 @@ TEST_P(TestDPCTLSyclPlatformInterface, ChkGetBackend)
     check_platform_backend(PRef);
 }
 
+TEST_P(TestDPCTLSyclPlatformInterface, ChkGetDefaultContext)
+{
+    check_platform_default_context(PRef);
+}
+
 TEST_P(TestDPCTLSyclPlatformInterface, ChkCopy)
 {
     DPCTLSyclPlatformRef Copied_PRef = nullptr;
@@ -342,6 +358,15 @@ TEST(TestGetPlatforms, Chk)
     EXPECT_NO_FATAL_FAILURE(DPCTLPlatformVector_Delete(PVRef));
 }
 
+TEST(TestNullPlatform, ChkGetDefaultConext)
+{
+    DPCTLSyclPlatformRef NullPRef = nullptr;
+    DPCTLSyclContextRef CRef = nullptr;
+
+    EXPECT_NO_FATAL_FAILURE(CRef = DPCTLPlatform_GetDefaultContext(NullPRef));
+    EXPECT_TRUE(CRef == nullptr);
+}
+
 INSTANTIATE_TEST_SUITE_P(DPCTLPlatformTests,
                          TestDPCTLSyclPlatformInterface,
                          ::testing::Values("opencl",