Skip to content

Commit b3ead6f

Browse files
committed
Add check that backend types are the same in _CallPeerAccess
1 parent f78c7f2 commit b3ead6f

File tree

1 file changed

+10
-9
lines changed

1 file changed

+10
-9
lines changed

libsyclinterface/source/dpctl_sycl_device_interface.cpp

+10-9
Original file line numberDiff line numberDiff line change
@@ -908,17 +908,18 @@ bool _CallPeerAccess(device dev, device peer)
908908
auto BE1 = dev.get_backend();
909909
auto BE2 = peer.get_backend();
910910

911-
if ((BE1 != sycl::backend::ext_oneapi_level_zero &&
912-
BE1 != sycl::backend::ext_oneapi_cuda &&
913-
BE1 != sycl::backend::ext_oneapi_hip) ||
914-
(BE2 != sycl::backend::ext_oneapi_level_zero &&
915-
BE2 != sycl::backend::ext_oneapi_cuda &&
916-
BE2 != sycl::backend::ext_oneapi_hip) ||
917-
(dev == peer))
911+
if ((BE1 == BE2) &&
912+
(BE1 == sycl::backend::ext_oneapi_level_zero ||
913+
BE1 == sycl::backend::ext_oneapi_cuda ||
914+
BE1 == sycl::backend::ext_oneapi_hip) &&
915+
(BE2 == sycl::backend::ext_oneapi_level_zero ||
916+
BE2 == sycl::backend::ext_oneapi_cuda ||
917+
BE2 == sycl::backend::ext_oneapi_hip) &&
918+
(dev != peer))
918919
{
919-
return false;
920+
return true;
920921
}
921-
return true;
922+
return false;
922923
}
923924

924925
bool DPCTLDevice_CanAccessPeer(__dpctl_keep const DPCTLSyclDeviceRef DRef,

0 commit comments

Comments
 (0)