Fix linear interop memory and L0 V1 adapter leaks. (#18353)

This patch fixes the mapping of interop memory to a linear range
represented by a `void*`. The SYCL Bindless Images spec is clarified
with wording to indicate which free APIs should be used on mapped
imported memory.

Using `sycl::free` for freeing mapped imported linear memory regions
does not work for the LevelZero adapter, as the backend needs to call
`zeMemFree` directly - it cannot go through the regular `sycl::free`
code as that will use UMF free functions by default. This is invalid for
memory regions mapped using `map_external_linear_memory`.

The `unmap_external_linear_memory` SYCL API has been added to the
Bindless Images specification to remedy this problem. An
`unmap_external_image_memory` has also been added.

This patch also introduces an E2E test which verifies that a Vulkan
buffer's memory can be correctly imported into SYCL and its data
retrieved from and written to within a SYCL kernel by using purely USM
pointers (i.e. without using bindless images). This is a step towards
extending the test coverage of interop functionality currently in the
Bindless Images extension, with the goal being at some point splitting
the interop functionality into one or more separate extensions.

Two other fixes have been made in the LevelZero UR adapter.

A leaked `ze_image_handle_t` object has been fixed in the LevelZero V1
adapter. The previous implementation incorrectly reinterpreted bindless
memory handles as `ur_mem_handle_t` types. The implementation of
`urBindlessImagesImageFreeExp` is now unified between V1 and V2,
removing the leak. As such the `level_zero/v2/image.cpp` file has been
removed.

The `urMemoryHandle` member of `ur_ze_external_memory_data` has been
removed. Aside from being incorrectly reinterpreted from
`ur_bindless_mem_handle_t`, the LevelZero adapter does not need to track
the memory handle for external memory resources.

Author: przemektmalon

include/ur_api.h

@@ -142,6 +142,7 @@ Enums
     * ${X}_FUNCTION_BINDLESS_IMAGES_IMPORT_EXTERNAL_MEMORY_EXP
     * ${X}_FUNCTION_BINDLESS_IMAGES_MAP_EXTERNAL_ARRAY_EXP
     * ${X}_FUNCTION_BINDLESS_IMAGES_RELEASE_EXTERNAL_MEMORY_EXP
+    * ${X}_FUNCTION_BINDLESS_IMAGES_FREE_MAPPED_LINEAR_MEMORY_EXP
     * ${X}_FUNCTION_BINDLESS_IMAGES_IMPORT_EXTERNAL_SEMAPHORE_EXP
     * ${X}_FUNCTION_BINDLESS_IMAGES_RELEASE_EXTERNAL_SEMAPHORE_EXP
     * ${X}_FUNCTION_BINDLESS_IMAGES_WAIT_EXTERNAL_SEMAPHORE_EXP
@@ -198,6 +199,7 @@ Functions
    * ${x}BindlessImagesMapExternalArrayExp
    * ${x}BindlessImagesMapExternalLinearMemoryExp
    * ${x}BindlessImagesReleaseExternalMemoryExp
+   * ${x}BindlessImagesFreeMappedLinearMemoryExp
    * ${x}BindlessImagesImportExternalSemaphoreExp
    * ${x}BindlessImagesReleaseExternalSemaphoreExp
    * ${x}BindlessImagesWaitExternalSemaphoreExp
@@ -286,6 +288,8 @@ Changelog
 |          ||  - GetImageUnsampledHandleSupportExp                       |
 |          ||  - GetImageSampledHandleSupportExp                         |
 +----------+-------------------------------------------------------------+
+| 23.0     | Added BindlessImagesFreeMappedLinearMemory function.        |
++----------+-------------------------------------------------------------+
 
 Contributors
 --------------------------------------------------------------------------------

include/ur_api_funcs.def

@@ -901,6 +901,29 @@ returns:
     - $X_RESULT_ERROR_INVALID_VALUE
 --- #--------------------------------------------------------------------------
 type: function
+desc: "Free a linear memory region mapped using MapExternalLinearMemoryExp"
+class: $xBindlessImages
+name: FreeMappedLinearMemoryExp
+ordinal: "0"
+analogue:
+    - "**cuMemFree**"
+    - "**zeMemFree**"
+params:
+    - type: $x_context_handle_t
+      name: hContext
+      desc: "[in] handle of the context object"
+    - type: $x_device_handle_t
+      name: hDevice
+      desc: "[in] handle of the device object"
+    - type: void *
+      name: pMem
+      desc: "[in][release] pointer to mapped linear memory region to be freed"
+returns:
+    - $X_RESULT_ERROR_INVALID_CONTEXT
+    - $X_RESULT_ERROR_INVALID_NULL_POINTER:
+        - "`pMem == NULL`"
+--- #--------------------------------------------------------------------------
+type: function
 desc: "Import an external semaphore"
 class: $xBindlessImages
 name: ImportExternalSemaphoreExp

include/ur_ddi.h

@@ -658,6 +658,9 @@ etors:
 - name: BINDLESS_IMAGES_GET_IMAGE_MEMORY_HANDLE_TYPE_SUPPORT_EXP
   desc: Enumerator for $xBindlessImagesGetImageMemoryHandleTypeSupportExp
   value: '270'
+- name: BINDLESS_IMAGES_FREE_MAPPED_LINEAR_MEMORY_EXP
+  desc: Enumerator for $xBindlessImagesFreeMappedLinearMemoryExp
+  value: '271'
 ---
 type: enum
 desc: Defines structure types

include/ur_print.h

@@ -1605,6 +1605,25 @@ UR_APIEXPORT ur_result_t UR_APICALL urBindlessImagesReleaseExternalMemoryExp(
   return UR_RESULT_SUCCESS;
 }
 
+UR_APIEXPORT ur_result_t UR_APICALL urBindlessImagesFreeMappedLinearMemoryExp(
+    ur_context_handle_t hContext, ur_device_handle_t hDevice, void *pMem) {
+  UR_ASSERT(std::find(hContext->getDevices().begin(),
+                      hContext->getDevices().end(),
+                      hDevice) != hContext->getDevices().end(),
+            UR_RESULT_ERROR_INVALID_CONTEXT);
+  UR_ASSERT(pMem, UR_RESULT_ERROR_INVALID_NULL_POINTER);
+
+  try {
+    ScopedContext Active(hDevice);
+    UR_CHECK_ERROR(cuMemFree(reinterpret_cast<CUdeviceptr>(pMem)));
+  } catch (ur_result_t Err) {
+    return Err;
+  } catch (...) {
+    return UR_RESULT_ERROR_UNKNOWN;
+  }
+  return UR_RESULT_SUCCESS;
+}
+
 UR_APIEXPORT ur_result_t UR_APICALL urBindlessImagesImportExternalSemaphoreExp(
     ur_context_handle_t hContext, ur_device_handle_t hDevice,
     ur_exp_external_semaphore_type_t semHandleType,

include/ur_print.hpp

@@ -344,6 +344,8 @@ UR_DLLEXPORT ur_result_t UR_APICALL urGetBindlessImagesExpProcAddrTable(
       urBindlessImagesMapExternalLinearMemoryExp;
   pDdiTable->pfnReleaseExternalMemoryExp =
       urBindlessImagesReleaseExternalMemoryExp;
+  pDdiTable->pfnFreeMappedLinearMemoryExp =
+      urBindlessImagesFreeMappedLinearMemoryExp;
   pDdiTable->pfnImportExternalSemaphoreExp =
       urBindlessImagesImportExternalSemaphoreExp;
   pDdiTable->pfnReleaseExternalSemaphoreExp =