@@ -16,9 +16,9 @@ namespace syclext = sycl::ext::oneapi::experimental;
1616constexpr size_t NumberOfDevices = 3 ;
1717
1818std::array<ur_device_handle_t , NumberOfDevices> GlobalDevicesHandle{
19- mock::createDummyHandle<ur_device_handle_t >(),
20- mock::createDummyHandle<ur_device_handle_t >(),
21- mock::createDummyHandle<ur_device_handle_t >(),
19+ mock::createDummyHandle<ur_device_handle_t >(),
20+ mock::createDummyHandle<ur_device_handle_t >(),
21+ mock::createDummyHandle<ur_device_handle_t >(),
2222};
2323
2424ur_result_t setup_urDeviceGet (void *pParams) {
@@ -37,107 +37,111 @@ ur_result_t setup_urDeviceGet(void *pParams) {
3737}
3838ur_result_t setup_urDeviceGetInfo (void *pParams) {
3939 auto params = *static_cast <ur_device_get_info_params_t *>(pParams);
40- switch (*params.ppropName ){
41- case UR_DEVICE_INFO_VIRTUAL_MEMORY_SUPPORT:{
42- if (*params.ppPropValue ) {
43- if (*params.phDevice == GlobalDevicesHandle[0 ]){
44- return UR_RESULT_ERROR_UNSUPPORTED_FEATURE;
45- }
40+ switch (*params.ppropName ) {
41+ case UR_DEVICE_INFO_VIRTUAL_MEMORY_SUPPORT: {
42+ if (*params.ppPropValue ) {
43+ if (*params.phDevice == GlobalDevicesHandle[0 ]) {
44+ return UR_RESULT_ERROR_UNSUPPORTED_FEATURE;
4645 }
47- break ;
48- }
49- default :{
50- break ;
5146 }
47+ break ;
48+ }
49+ default : {
50+ break ;
51+ }
5252 }
5353 return UR_RESULT_SUCCESS;
5454}
5555
5656TEST (VirtualMemoryMultipleDevices, ThrowExceptionForGetMemGranularityContext) {
57-
57+
5858 sycl::unittest::UrMock<> Mock;
59- mock::getCallbacks ().set_replace_callback (" urDeviceGet" ,
60- &setup_urDeviceGet);
59+ mock::getCallbacks ().set_replace_callback (" urDeviceGet" , &setup_urDeviceGet);
6160 mock::getCallbacks ().set_replace_callback (" urDeviceGetInfo" ,
62- &setup_urDeviceGetInfo);
61+ &setup_urDeviceGetInfo);
6362 sycl::platform Platform = sycl::platform ();
6463 sycl::context Context{Platform};
6564
6665 try {
67- syclext::get_mem_granularity (Context, syclext::granularity_mode::recommended);
66+ syclext::get_mem_granularity (Context,
67+ syclext::granularity_mode::recommended);
6868 } catch (sycl::exception &e) {
6969 EXPECT_EQ (e.code (), sycl::errc::feature_not_supported);
70- EXPECT_STREQ (e.what (), " One or more devices in the context does not support aspect::ext_oneapi_virtual_mem." );
70+ EXPECT_STREQ (e.what (), " One or more devices in the context does not "
71+ " support aspect::ext_oneapi_virtual_mem." );
7172 }
7273
7374 try {
7475 syclext::get_mem_granularity (Context, syclext::granularity_mode::minimum);
7576 } catch (sycl::exception &e) {
7677 EXPECT_EQ (e.code (), sycl::errc::feature_not_supported);
77- EXPECT_STREQ (e.what (), " One or more devices in the context does not support aspect::ext_oneapi_virtual_mem." );
78+ EXPECT_STREQ (e.what (), " One or more devices in the context does not "
79+ " support aspect::ext_oneapi_virtual_mem." );
7880 }
7981}
8082
8183TEST (VirtualMemoryMultipleDevices, ThrowExceptionForGetMemGranularityDevice) {
82-
84+
8385 sycl::unittest::UrMock<> Mock;
84- mock::getCallbacks ().set_replace_callback (" urDeviceGet" ,
85- &setup_urDeviceGet);
86+ mock::getCallbacks ().set_replace_callback (" urDeviceGet" , &setup_urDeviceGet);
8687 mock::getCallbacks ().set_replace_callback (" urDeviceGetInfo" ,
87- &setup_urDeviceGetInfo);
88+ &setup_urDeviceGetInfo);
8889 sycl::platform Platform = sycl::platform ();
8990 sycl::context Context{Platform};
9091
9192 try {
92- syclext::get_mem_granularity (Context.get_devices ().front (), Context, syclext::granularity_mode::recommended);
93+ syclext::get_mem_granularity (Context.get_devices ().front (), Context,
94+ syclext::granularity_mode::recommended);
9395 } catch (sycl::exception &e) {
9496 EXPECT_EQ (e.code (), sycl::errc::feature_not_supported);
95- EXPECT_STREQ (e.what (), " Device does not support aspect::ext_oneapi_virtual_mem." );
97+ EXPECT_STREQ (e.what (),
98+ " Device does not support aspect::ext_oneapi_virtual_mem." );
9699 }
97100
98101 try {
99- syclext::get_mem_granularity (Context.get_devices ().front (), Context, syclext::granularity_mode::minimum);
102+ syclext::get_mem_granularity (Context.get_devices ().front (), Context,
103+ syclext::granularity_mode::minimum);
100104 } catch (sycl::exception &e) {
101105 EXPECT_EQ (e.code (), sycl::errc::feature_not_supported);
102- EXPECT_STREQ (e.what (), " Device does not support aspect::ext_oneapi_virtual_mem." );
106+ EXPECT_STREQ (e.what (),
107+ " Device does not support aspect::ext_oneapi_virtual_mem." );
103108 }
104109}
105110
106-
107111TEST (VirtualMemoryMultipleDevices, ReserveVirtualMemoryRange) {
108112
109113 sycl::unittest::UrMock<> Mock;
110- mock::getCallbacks ().set_replace_callback (" urDeviceGet" ,
111- &setup_urDeviceGet);
114+ mock::getCallbacks ().set_replace_callback (" urDeviceGet" , &setup_urDeviceGet);
112115 mock::getCallbacks ().set_replace_callback (" urDeviceGetInfo" ,
113- &setup_urDeviceGetInfo);
116+ &setup_urDeviceGetInfo);
114117 sycl::platform Platform = sycl::platform ();
115118 sycl::context Context{Platform};
116119
117120 try {
118121 syclext::reserve_virtual_mem (0 , sizeof (int ), Context);
119122 } catch (sycl::exception &e) {
120123 EXPECT_EQ (e.code (), sycl::errc::feature_not_supported);
121- EXPECT_STREQ (e.what (), " One or more devices in the supplied context does not support "
122- " aspect::ext_oneapi_virtual_mem." );
124+ EXPECT_STREQ (e.what (),
125+ " One or more devices in the supplied context does not support "
126+ " aspect::ext_oneapi_virtual_mem." );
123127 }
124128}
125129
126-
127130TEST (VirtualMemoryMultipleDevices, ReservePhysicalMemory) {
128131
129132 sycl::unittest::UrMock<> Mock;
130- mock::getCallbacks ().set_replace_callback (" urDeviceGet" ,
131- &setup_urDeviceGet);
133+ mock::getCallbacks ().set_replace_callback (" urDeviceGet" , &setup_urDeviceGet);
132134 mock::getCallbacks ().set_replace_callback (" urDeviceGetInfo" ,
133- &setup_urDeviceGetInfo);
135+ &setup_urDeviceGetInfo);
134136 sycl::platform Platform = sycl::platform ();
135137 sycl::context Context{Platform};
136138
137139 try {
138- syclext::physical_mem PhysicalMem{Context.get_devices ().front (), Context, sizeof (int )};
140+ syclext::physical_mem PhysicalMem{Context.get_devices ().front (), Context,
141+ sizeof (int )};
139142 } catch (sycl::exception &e) {
140143 EXPECT_EQ (e.code (), sycl::errc::feature_not_supported);
141- EXPECT_STREQ (e.what (), " Device does not support aspect::ext_oneapi_virtual_mem." );
144+ EXPECT_STREQ (e.what (),
145+ " Device does not support aspect::ext_oneapi_virtual_mem." );
142146 }
143147}
0 commit comments