Reorganization directory structure [1/n]

Change-Id: Id1a94577437a4826a32411869f516fec20314ec0
2025-12-26 23:33:20 +08:00 · 2020-02-22 21:54:11 +01:00
parent 247cc953d1
commit fa8e720f9e
660 changed files with 3 additions and 3 deletions
--- a/opencl/source/api/dispatch.cpp
+++ b/opencl/source/api/dispatch.cpp
@@ -0,0 +1,215 @@
+/*
+ * Copyright (C) 2017-2020 Intel Corporation
+ *
+ * SPDX-License-Identifier: MIT
+ *
+ */
+
+#include "dispatch.h"
+
+#include "api.h"
+
+SDispatchTable icdGlobalDispatchTable =
+    {
+        clGetPlatformIDs,
+        clGetPlatformInfo,
+        clGetDeviceIDs,
+        clGetDeviceInfo,
+        clCreateContext,
+        clCreateContextFromType,
+        clRetainContext,
+        clReleaseContext,
+        clGetContextInfo,
+        clCreateCommandQueue,
+        clRetainCommandQueue,
+        clReleaseCommandQueue,
+        clGetCommandQueueInfo,
+        clSetCommandQueueProperty,
+        clCreateBuffer,
+        clCreateImage2D,
+        clCreateImage3D,
+        clRetainMemObject,
+        clReleaseMemObject,
+        clGetSupportedImageFormats,
+        clGetMemObjectInfo,
+        clGetImageInfo,
+        clCreateSampler,
+        clRetainSampler,
+        clReleaseSampler,
+        clGetSamplerInfo,
+        clCreateProgramWithSource,
+        clCreateProgramWithBinary,
+        clRetainProgram,
+        clReleaseProgram,
+        clBuildProgram,
+        clUnloadCompiler,
+        clGetProgramInfo,
+        clGetProgramBuildInfo,
+        clCreateKernel,
+        clCreateKernelsInProgram,
+        clRetainKernel,
+        clReleaseKernel,
+        clSetKernelArg,
+        clGetKernelInfo,
+        clGetKernelWorkGroupInfo,
+        clWaitForEvents,
+        clGetEventInfo,
+        clRetainEvent,
+        clReleaseEvent,
+        clGetEventProfilingInfo,
+        clFlush,
+        clFinish,
+        clEnqueueReadBuffer,
+        clEnqueueWriteBuffer,
+        clEnqueueCopyBuffer,
+        clEnqueueReadImage,
+        clEnqueueWriteImage,
+        clEnqueueCopyImage,
+        clEnqueueCopyImageToBuffer,
+        clEnqueueCopyBufferToImage,
+        clEnqueueMapBuffer,
+        clEnqueueMapImage,
+        clEnqueueUnmapMemObject,
+        clEnqueueNDRangeKernel,
+        clEnqueueTask,
+        clEnqueueNativeKernel,
+        clEnqueueMarker,
+        clEnqueueWaitForEvents,
+        clEnqueueBarrier,
+        clGetExtensionFunctionAddress,
+
+        /* cl_khr_gl_sharing */
+        nullptr,
+        nullptr,
+        nullptr,
+        nullptr,
+        nullptr,
+        nullptr,
+        nullptr,
+        nullptr,
+        nullptr,
+
+        /* cl_khr_d3d10_sharing */
+        nullptr, // clGetDeviceIDsFromD3D10KHR,
+        nullptr, // clCreateFromD3D10BufferKHR,
+        nullptr, // clCreateFromD3D10Texture2DKHR,
+        nullptr, // clCreateFromD3D10Texture3DKHR,
+        nullptr, // clEnqueueAcquireD3D10ObjectsKHR,
+        nullptr, // clEnqueueReleaseD3D10ObjectsKHR,
+
+        /* OpenCL 1.1 */
+        clSetEventCallback,
+        clCreateSubBuffer,
+        clSetMemObjectDestructorCallback,
+        clCreateUserEvent,
+        clSetUserEventStatus,
+        clEnqueueReadBufferRect,
+        clEnqueueWriteBufferRect,
+        clEnqueueCopyBufferRect,
+
+        /* cl_ext_device_fission */
+        nullptr, //clCreateSubDevicesEXT,
+        nullptr, //clRetainDeviceEXT,
+        nullptr, //clReleaseDeviceEXT,
+
+        /* cl_khr_gl_event */
+        nullptr,
+
+        /* OpenCL 1.2 */
+        clCreateSubDevices,
+        clRetainDevice,
+        clReleaseDevice,
+        clCreateImage,
+        clCreateProgramWithBuiltInKernels,
+        clCompileProgram,
+        clLinkProgram,
+        clUnloadPlatformCompiler,
+        clGetKernelArgInfo,
+        clEnqueueFillBuffer,
+        clEnqueueFillImage,
+        clEnqueueMigrateMemObjects,
+        clEnqueueMarkerWithWaitList,
+        clEnqueueBarrierWithWaitList,
+        clGetExtensionFunctionAddressForPlatform,
+        nullptr,
+
+        /* cl_khr_d3d11_sharing */
+        nullptr, // clGetDeviceIDsFromD3D11KHR,
+        nullptr, // clCreateFromD3D11BufferKHR,
+        nullptr, // clCreateFromD3D11Texture2DKHR,
+        nullptr, // clCreateFromD3D11Texture3DKHR,
+        nullptr, // clCreateFromDX9MediaSurfaceKHR,
+        nullptr, // clEnqueueAcquireD3D11ObjectsKHR,
+        nullptr, // clEnqueueReleaseD3D11ObjectsKHR,
+
+        /* cl_khr_dx9_media_sharing */
+        nullptr, // clGetDeviceIDsFromDX9MediaAdapterKHR,
+        nullptr, // clEnqueueAcquireDX9MediaSurfacesKHR,
+        nullptr, // clEnqueueReleaseDX9MediaSurfacesKHR,
+
+        /* cl_khr_egl_image */
+        nullptr, //clCreateFromEGLImageKHR,
+        nullptr, //clEnqueueAcquireEGLObjectsKHR,
+        nullptr, //clEnqueueReleaseEGLObjectsKHR,
+
+        /* cl_khr_egl_event */
+        nullptr, //clCreateEventFromEGLSyncKHR,
+
+        /* OpenCL 2.0 */
+        clCreateCommandQueueWithProperties,
+        clCreatePipe,
+        clGetPipeInfo,
+        clSVMAlloc,
+        clSVMFree,
+        clEnqueueSVMFree,
+        clEnqueueSVMMemcpy,
+        clEnqueueSVMMemFill,
+        clEnqueueSVMMap,
+        clEnqueueSVMUnmap,
+        clCreateSamplerWithProperties,
+        clSetKernelArgSVMPointer,
+        clSetKernelExecInfo,
+        clGetKernelSubGroupInfoKHR,
+
+        /* OpenCL 2.1 */
+        clCloneKernel,
+        clCreateProgramWithIL,
+        clEnqueueSVMMigrateMem,
+        clGetDeviceAndHostTimer,
+        clGetHostTimer,
+        clGetKernelSubGroupInfo,
+        clSetDefaultDeviceCommandQueue,
+
+        /* OpenCL 2.2 */
+        clSetProgramSpecializationConstant};
+
+SCRTDispatchTable crtGlobalDispatchTable = {
+    clGetKernelArgInfo,
+
+    nullptr, // clGetDeviceIDsFromDX9INTEL,
+    nullptr, // clCreateFromDX9MediaSurfaceINTEL,
+    nullptr, // clEnqueueAcquireDX9ObjectsINTEL,
+    nullptr, // clEnqueueReleaseDX9ObjectsINTEL,
+    clGetImageParamsINTEL,
+    clCreatePerfCountersCommandQueueINTEL,
+
+    clCreateAcceleratorINTEL,
+    clGetAcceleratorInfoINTEL,
+    clRetainAcceleratorINTEL,
+    clReleaseAcceleratorINTEL,
+
+    nullptr,
+    nullptr,
+
+    nullptr,
+    nullptr,
+    nullptr,
+    nullptr,
+
+    nullptr,
+    nullptr,
+    nullptr,
+    nullptr,
+    clSetPerformanceConfigurationINTEL};
+
+SEntryPointsTable globalDispatchTable = {&icdGlobalDispatchTable, &crtGlobalDispatchTable};