Maosu Zhao

[DeviceSanitizer] Support detecting out-of-bounds error on DeviceGlobals

5

UR part: https://github.com/oneapi-src/unified-runtime/pull/1354

[DeviceSanitizer] Do sanitize for device globals in AddressSanitizer pass

2

Now UR already implemented API "urProgramGetGlobalVariablePointer", so we can use it to query the size of device globals and remove "__AsanDeviceGlobalCount". UR Part: https://github.com/oneapi-src/unified-runtime/pull/1584

L0 GPU runtime will divide the device memory address space equally among the all gpu devices. So, if there are multiple gpu devices, device sanitizer may not be able to...

[DeviceSanitizer] Support detecting out-of-bounds errors on sycl::buffer

3

As we discussed before, we intercepted buffer with usm for short-term solution. For long-term, we will draft a new ocl extension to allow user to create buffer with fixed address....

L0 GPU runtime will divide the device memory address space equally among the all gpu devices. So, if there are multiple gpu devices, device sanitizer may not be able to...

Now UR already implemented API "urProgramGetGlobalVariablePointer", so we can use it to query the size of device globals and remove "__AsanDeviceGlobalCount". SYCLOS Part: https://github.com/intel/llvm/pull/13678

[DeviceSanitizer] Handle mem buffer is created with flag COPY_HOST_POINTER

2

SYCLOS Part for pre-ci: https://github.com/intel/llvm/pull/14551

Also maintain an internal ref count of ContextInfo. SYCLOS Part: https://github.com/intel/llvm/pull/14378