Adds C-API tests for composite devices

Author: ndgrigorian

libsyclinterface/tests/test_sycl_device_aspects.cpp

@@ -127,7 +127,11 @@ auto build_params()
             std::make_pair("usm_atomic_shared_allocations",
                            sycl::aspect::usm_atomic_shared_allocations),
             std::make_pair("host_debuggable", sycl::aspect::host_debuggable),
-            std::make_pair("emulated", sycl::aspect::emulated));
+            std::make_pair("emulated", sycl::aspect::emulated),
+            std::make_pair("is_component",
+                           sycl::aspect::ext_oneapi_is_composite),
+            std::make_pair("is_composite",
+                           sycl::aspect::ext_oneapi_is_component));
 
     auto pairs =
         build_param_pairs<const char *, std::pair<const char *, sycl::aspect>,

libsyclinterface/tests/test_sycl_device_manager.cpp

@@ -316,3 +316,71 @@ TEST_F(TestDPCTLDeviceMgrNullReference, ChkGetPositionInDevices)
     EXPECT_NO_FATAL_FAILURE(
         DPCTLDeviceMgr_GetPositionInDevices(nullDRef, mask));
 }
+
+struct TestDPCTLGetCompositeDevices : public ::testing::Test
+{
+    DPCTLDeviceVectorRef DV = nullptr;
+    size_t nDevices = 0;
+
+    TestDPCTLGetCompositeDevices()
+    {
+        EXPECT_NO_FATAL_FAILURE(DV = DPCTLDeviceMgr_GetCompositeDevices());
+        EXPECT_TRUE(DV != nullptr);
+        EXPECT_NO_FATAL_FAILURE(nDevices = DPCTLDeviceVector_Size(DV));
+    }
+
+    void SetUp()
+    {
+        if (!nDevices) {
+            GTEST_SKIP_("Skipping as no composite devices available");
+        }
+    }
+
+    ~TestDPCTLGetCompositeDevices()
+    {
+        EXPECT_NO_FATAL_FAILURE(DPCTLDeviceVector_Clear(DV));
+        EXPECT_NO_FATAL_FAILURE(DPCTLDeviceVector_Delete(DV));
+    }
+};
+
+TEST_F(TestDPCTLGetCompositeDevices, ChkGetAt)
+{
+    for (auto i = 0ul; i < nDevices; ++i) {
+        DPCTLSyclDeviceRef DRef = nullptr;
+        EXPECT_NO_FATAL_FAILURE(DRef = DPCTLDeviceVector_GetAt(DV, i));
+        ASSERT_TRUE(DRef != nullptr);
+    }
+}
+
+TEST_F(TestDPCTLGetCompositeDevices, ChkCompositeAspect)
+{
+    for (auto i = 0ul; i < nDevices; ++i) {
+        DPCTLSyclDeviceRef DRef = nullptr;
+        EXPECT_NO_FATAL_FAILURE(DRef = DPCTLDeviceVector_GetAt(DV, i));
+        ASSERT_TRUE(DRef != nullptr);
+        ASSERT_TRUE(
+            DPCTLDevice_HasAspect(DRef, DPCTLSyclAspectType::is_composite));
+    }
+}
+
+TEST_F(TestDPCTLGetCompositeDevices, ChkComponentDevices)
+{
+    for (auto i = 0ul; i < nDevices; ++i) {
+        DPCTLSyclDeviceRef DRef = nullptr;
+        EXPECT_NO_FATAL_FAILURE(DRef = DPCTLDeviceVector_GetAt(DV, i));
+        ASSERT_TRUE(DRef != nullptr);
+        DPCTLDeviceVectorRef CDV = nullptr;
+        size_t nComponents = 0;
+        EXPECT_NO_FATAL_FAILURE(CDV = DPCTLDevice_GetComponentDevices(DRef));
+        EXPECT_NO_FATAL_FAILURE(nComponents = DPCTLDeviceVector_Size(CDV));
+        for (auto j = 0ul; j < nComponents; ++j) {
+            DPCTLSyclDeviceRef CDRef = nullptr;
+            EXPECT_NO_FATAL_FAILURE(CDRef = DPCTLDeviceVector_GetAt(CDV, j));
+            ASSERT_TRUE(CDRef != nullptr);
+            ASSERT_TRUE(DPCTLDevice_HasAspect(
+                CDRef, DPCTLSyclAspectType::is_component));
+        }
+        EXPECT_NO_FATAL_FAILURE(DPCTLDeviceVector_Clear(CDV));
+        EXPECT_NO_FATAL_FAILURE(DPCTLDeviceVector_Delete(CDV));
+    }
+}