[SYCLomatic] Add the 3 IPC APIs query API Mapping. (#2907)

Signed-off-by: Chen, Sheng S <sheng.s.chen@intel.com>

Author: ShengchenJ

clang/examples/DPCT/Runtime/cudaIpcCloseMemHandle.cu

@@ -0,0 +1,9 @@
+// Option: --use-experimental-features=level_zero
+#include <cuda.h>
+
+void test() {
+  void *ptr;
+  // Start
+  cudaIpcCloseMemHandle(ptr/*void **/);
+  // End
+}

clang/examples/DPCT/Runtime/cudaIpcGetMemHandle.cu

@@ -0,0 +1,10 @@
+// Option: --use-experimental-features=level_zero
+#include <cuda.h>
+
+void test() {
+  cudaIpcMemHandle_t *handle;
+  void *ptr;
+  // Start
+  cudaIpcGetMemHandle(handle/*cudaIpcMemHandle_t **/, ptr/*void **/);
+  // End
+}

clang/examples/DPCT/Runtime/cudaIpcOpenMemHandle.cu

@@ -0,0 +1,11 @@
+// Option: --use-experimental-features=level_zero
+
+#include <cuda.h>
+
+void test() {
+  cudaIpcMemHandle_t *handle;
+  void *ptr;
+  // Start
+  cudaIpcOpenMemHandle((void **)&ptr/*void ***/, *handle/*cudaIpcMemHandle_t*/, cudaIpcMemLazyEnablePeerAccess/*unsigned int*/);
+  // End
+}

clang/test/dpct/query_api_mapping/Runtime/test_ipc.cu

@@ -0,0 +1,18 @@
+// UNSUPPORTED: system-windows
+// RUN: dpct --cuda-include-path="%cuda-path/include" --query-api-mapping=cudaIpcOpenMemHandle | FileCheck %s -check-prefix=CUDA_IPC_OPEN_MEM_HANDLE
+// CUDA_IPC_OPEN_MEM_HANDLE: CUDA API:
+// CUDA_IPC_OPEN_MEM_HANDLE-NEXT:  cudaIpcOpenMemHandle((void **)&ptr/*void ***/, *handle/*cudaIpcMemHandle_t*/, cudaIpcMemLazyEnablePeerAccess/*unsigned int*/);
+// CUDA_IPC_OPEN_MEM_HANDLE-NEXT: Is migrated to (with the option --use-experimental-features=level_zero):
+// CUDA_IPC_OPEN_MEM_HANDLE-NEXT:  dpct::experimental::open_mem_ipc_handle(*handle, (void **)&ptr);
+
+// RUN: dpct --cuda-include-path="%cuda-path/include" --query-api-mapping=cudaIpcCloseMemHandle | FileCheck %s -check-prefix=CUDA_IPC_CLOSE_MEM_HANDLE
+// CUDA_IPC_CLOSE_MEM_HANDLE: CUDA API:
+// CUDA_IPC_CLOSE_MEM_HANDLE-NEXT:   cudaIpcCloseMemHandle(ptr/*void **/);
+// CUDA_IPC_CLOSE_MEM_HANDLE-NEXT: Is migrated to (with the option --use-experimental-features=level_zero):
+// CUDA_IPC_CLOSE_MEM_HANDLE-NEXT:  zeMemCloseIpcHandle(sycl::get_native<sycl::backend::ext_oneapi_level_zero>(dpct::get_current_device().get_context()), ptr);
+
+// RUN: dpct --cuda-include-path="%cuda-path/include" --query-api-mapping=cudaIpcGetMemHandle | FileCheck %s -check-prefix=CUDA_IPC_GET_MEM_HANDLE
+// CUDA_IPC_GET_MEM_HANDLE: CUDA API:
+// CUDA_IPC_GET_MEM_HANDLE-NEXT:  cudaIpcGetMemHandle(handle/*cudaIpcMemHandle_t **/, ptr/*void **/)
+// CUDA_IPC_GET_MEM_HANDLE-NEXT: Is migrated to (with the option --use-experimental-features=level_zero):
+// CUDA_IPC_GET_MEM_HANDLE-NEXT:  dpct::experimental::get_mem_ipc_handle(ptr, handle);

clang/test/dpct/query_api_mapping/test_all.cu

@@ -1376,6 +1376,9 @@
 // CHECK-NEXT: cudaHostUnregister
 // CHECK-NEXT: cudaImportExternalMemory
 // CHECK-NEXT: cudaImportExternalSemaphore
+// CHECK-NEXT: cudaIpcCloseMemHandle
+// CHECK-NEXT: cudaIpcGetMemHandle
+// CHECK-NEXT: cudaIpcOpenMemHandle
 // CHECK-NEXT: cudaLaunchCooperativeKernel
 // CHECK-NEXT: cudaLaunchKernel
 // CHECK-NEXT: cudaMalloc