From c79877c3ef022363ae472f51a91bb5135e1e3e82 Mon Sep 17 00:00:00 2001 From: Mateusz Jablonski Date: Mon, 27 Oct 2025 14:57:02 +0000 Subject: [PATCH] fix: add missing ZE_APICALL keyword Signed-off-by: Mateusz Jablonski --- .../api/core/ze_barrier_api_entrypoints.h | 6 +- .../api/core/ze_cmdlist_api_entrypoints.h | 34 +- .../api/core/ze_cmdqueue_api_entrypoints.h | 12 +- .../api/core/ze_context_api_entrypoints.h | 36 +-- level_zero/api/core/ze_copy_api_entrypoints.h | 24 +- .../api/core/ze_device_api_entrypoints.h | 46 +-- .../api/core/ze_driver_api_entrypoints.h | 26 +- .../api/core/ze_event_api_entrypoints.h | 44 +-- .../api/core/ze_fence_api_entrypoints.h | 12 +- .../api/core/ze_image_api_entrypoints.h | 8 +- .../api/core/ze_memory_api_entrypoints.h | 26 +- .../api/core/ze_module_api_entrypoints.h | 60 ++-- .../api/core/ze_sampler_api_entrypoints.h | 6 +- .../runtime/ze_runtime_all_api_entrypoints.h | 8 +- .../api/sysman/zes_sysman_api_entrypoints.h | 298 +++++++++--------- .../api/tools/zet_debug_api_entrypoints.h | 28 +- .../api/tools/zet_metric_api_entrypoints.h | 38 +-- .../api/tools/zet_module_api_entrypoints.h | 6 +- 18 files changed, 359 insertions(+), 359 deletions(-) diff --git a/level_zero/api/core/ze_barrier_api_entrypoints.h b/level_zero/api/core/ze_barrier_api_entrypoints.h index 6986745f9b..5f0a0f5964 100644 --- a/level_zero/api/core/ze_barrier_api_entrypoints.h +++ b/level_zero/api/core/ze_barrier_api_entrypoints.h @@ -14,7 +14,7 @@ #include "graph_captured_apis.h" namespace L0 { -ze_result_t zeCommandListAppendBarrier( +ze_result_t ZE_APICALL zeCommandListAppendBarrier( ze_command_list_handle_t hCommandList, ze_event_handle_t hSignalEvent, uint32_t numWaitEvents, @@ -28,7 +28,7 @@ ze_result_t zeCommandListAppendBarrier( return cmdList->appendBarrier(hSignalEvent, numWaitEvents, phWaitEvents, false); } -ze_result_t zeCommandListAppendMemoryRangesBarrier( +ze_result_t ZE_APICALL zeCommandListAppendMemoryRangesBarrier( ze_command_list_handle_t hCommandList, uint32_t numRanges, const size_t *pRangeSizes, @@ -45,7 +45,7 @@ ze_result_t zeCommandListAppendMemoryRangesBarrier( return L0::CommandList::fromHandle(hCommandList)->appendMemoryRangesBarrier(numRanges, pRangeSizes, pRanges, hSignalEvent, numWaitEvents, phWaitEvents); } -ze_result_t zeDeviceSystemBarrier( +ze_result_t ZE_APICALL zeDeviceSystemBarrier( ze_device_handle_t hDevice) { return L0::Device::fromHandle(hDevice)->systemBarrier(); } diff --git a/level_zero/api/core/ze_cmdlist_api_entrypoints.h b/level_zero/api/core/ze_cmdlist_api_entrypoints.h index ea3796e3f5..c7e1840d17 100644 --- a/level_zero/api/core/ze_cmdlist_api_entrypoints.h +++ b/level_zero/api/core/ze_cmdlist_api_entrypoints.h @@ -15,7 +15,7 @@ #include "graph_captured_apis.h" namespace L0 { -ze_result_t zeCommandListCreate( +ze_result_t ZE_APICALL zeCommandListCreate( ze_context_handle_t hContext, ze_device_handle_t hDevice, const ze_command_list_desc_t *desc, @@ -23,7 +23,7 @@ ze_result_t zeCommandListCreate( return L0::Context::fromHandle(hContext)->createCommandList(hDevice, desc, phCommandList); } -ze_result_t zeCommandListCreateImmediate( +ze_result_t ZE_APICALL zeCommandListCreateImmediate( ze_context_handle_t hContext, ze_device_handle_t hDevice, const ze_command_queue_desc_t *altdesc, @@ -31,22 +31,22 @@ ze_result_t zeCommandListCreateImmediate( return L0::Context::fromHandle(hContext)->createCommandListImmediate(hDevice, altdesc, phCommandList); } -ze_result_t zeCommandListDestroy( +ze_result_t ZE_APICALL zeCommandListDestroy( ze_command_list_handle_t hCommandList) { return L0::CommandList::fromHandle(hCommandList)->destroy(); } -ze_result_t zeCommandListClose( +ze_result_t ZE_APICALL zeCommandListClose( ze_command_list_handle_t hCommandList) { return L0::CommandList::fromHandle(hCommandList)->close(); } -ze_result_t zeCommandListReset( +ze_result_t ZE_APICALL zeCommandListReset( ze_command_list_handle_t hCommandList) { return L0::CommandList::fromHandle(hCommandList)->reset(); } -ze_result_t zeCommandListAppendWriteGlobalTimestamp( +ze_result_t ZE_APICALL zeCommandListAppendWriteGlobalTimestamp( ze_command_list_handle_t hCommandList, uint64_t *dstptr, ze_event_handle_t hSignalEvent, @@ -61,7 +61,7 @@ ze_result_t zeCommandListAppendWriteGlobalTimestamp( return cmdList->appendWriteGlobalTimestamp(dstptr, hSignalEvent, numWaitEvents, phWaitEvents); } -ze_result_t zeCommandListAppendQueryKernelTimestamps( +ze_result_t ZE_APICALL zeCommandListAppendQueryKernelTimestamps( ze_command_list_handle_t hCommandList, uint32_t numEvents, ze_event_handle_t *phEvents, @@ -79,37 +79,37 @@ ze_result_t zeCommandListAppendQueryKernelTimestamps( return cmdList->appendQueryKernelTimestamps(numEvents, phEvents, dstptr, pOffsets, hSignalEvent, numWaitEvents, phWaitEvents); } -ze_result_t zeCommandListGetDeviceHandle( +ze_result_t ZE_APICALL zeCommandListGetDeviceHandle( ze_command_list_handle_t hCommandList, ze_device_handle_t *phDevice) { return L0::CommandList::fromHandle(hCommandList)->getDeviceHandle(phDevice); } -ze_result_t zeCommandListGetContextHandle( +ze_result_t ZE_APICALL zeCommandListGetContextHandle( ze_command_list_handle_t hCommandList, ze_context_handle_t *phContext) { return L0::CommandList::fromHandle(hCommandList)->getContextHandle(phContext); } -ze_result_t zeCommandListGetOrdinal( +ze_result_t ZE_APICALL zeCommandListGetOrdinal( ze_command_list_handle_t hCommandList, uint32_t *pOrdinal) { return L0::CommandList::fromHandle(hCommandList)->getOrdinal(pOrdinal); } -ze_result_t zeCommandListImmediateGetIndex( +ze_result_t ZE_APICALL zeCommandListImmediateGetIndex( ze_command_list_handle_t hCommandListImmediate, uint32_t *pIndex) { return L0::CommandList::fromHandle(hCommandListImmediate)->getImmediateIndex(pIndex); } -ze_result_t zeCommandListIsImmediate( +ze_result_t ZE_APICALL zeCommandListIsImmediate( ze_command_list_handle_t hCommandList, ze_bool_t *pIsImmediate) { return L0::CommandList::fromHandle(hCommandList)->isImmediate(pIsImmediate); } -ze_result_t zeCommandListCreateCloneExp( +ze_result_t ZE_APICALL zeCommandListCreateCloneExp( ze_command_list_handle_t hCommandList, ze_command_list_handle_t *phClonedCommandList) { return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; @@ -125,7 +125,7 @@ ze_result_t ZE_APICALL zeCommandListImmediateAppendCommandListsExp( return L0::CommandList::fromHandle(hCommandListImmediate)->appendCommandLists(numCommandLists, phCommandLists, hSignalEvent, numWaitEvents, phWaitEvents); } -ze_result_t zeCommandListAppendSignalExternalSemaphoreExt( +ze_result_t ZE_APICALL zeCommandListAppendSignalExternalSemaphoreExt( ze_command_list_handle_t hCommandList, uint32_t numSemaphores, ze_external_semaphore_ext_handle_t *phSemaphores, @@ -142,7 +142,7 @@ ze_result_t zeCommandListAppendSignalExternalSemaphoreExt( return cmdList->appendSignalExternalSemaphores(numSemaphores, phSemaphores, signalParams, hSignalEvent, numWaitEvents, phWaitEvents); } -ze_result_t zeCommandListAppendWaitExternalSemaphoreExt( +ze_result_t ZE_APICALL zeCommandListAppendWaitExternalSemaphoreExt( ze_command_list_handle_t hCommandList, uint32_t numSemaphores, ze_external_semaphore_ext_handle_t *phSemaphores, @@ -159,7 +159,7 @@ ze_result_t zeCommandListAppendWaitExternalSemaphoreExt( return cmdList->appendWaitExternalSemaphores(numSemaphores, phSemaphores, waitParams, hSignalEvent, numWaitEvents, phWaitEvents); } -ze_result_t zeCommandListAppendLaunchKernelWithArguments( +ze_result_t ZE_APICALL zeCommandListAppendLaunchKernelWithArguments( ze_command_list_handle_t hCommandList, ze_kernel_handle_t hKernel, const ze_group_count_t groupCounts, @@ -180,7 +180,7 @@ ze_result_t zeCommandListAppendLaunchKernelWithArguments( return L0::CommandList::fromHandle(hCommandList)->appendLaunchKernelWithArguments(hKernel, groupCounts, groupSizes, pArguments, pNext, hSignalEvent, numWaitEvents, phWaitEvents); } -ze_result_t zeCommandListAppendLaunchKernelWithParameters( +ze_result_t ZE_APICALL zeCommandListAppendLaunchKernelWithParameters( ze_command_list_handle_t hCommandList, ze_kernel_handle_t hKernel, const ze_group_count_t *pGroupCounts, diff --git a/level_zero/api/core/ze_cmdqueue_api_entrypoints.h b/level_zero/api/core/ze_cmdqueue_api_entrypoints.h index 8b2b3118ad..b1b6041c32 100644 --- a/level_zero/api/core/ze_cmdqueue_api_entrypoints.h +++ b/level_zero/api/core/ze_cmdqueue_api_entrypoints.h @@ -12,7 +12,7 @@ #include namespace L0 { -ze_result_t zeCommandQueueCreate( +ze_result_t ZE_APICALL zeCommandQueueCreate( ze_context_handle_t hContext, ze_device_handle_t hDevice, const ze_command_queue_desc_t *desc, @@ -20,12 +20,12 @@ ze_result_t zeCommandQueueCreate( return L0::Context::fromHandle(hContext)->createCommandQueue(hDevice, desc, phCommandQueue); } -ze_result_t zeCommandQueueDestroy( +ze_result_t ZE_APICALL zeCommandQueueDestroy( ze_command_queue_handle_t hCommandQueue) { return L0::CommandQueue::fromHandle(hCommandQueue)->destroy(); } -ze_result_t zeCommandQueueExecuteCommandLists( +ze_result_t ZE_APICALL zeCommandQueueExecuteCommandLists( ze_command_queue_handle_t hCommandQueue, uint32_t numCommandLists, ze_command_list_handle_t *phCommandLists, @@ -33,19 +33,19 @@ ze_result_t zeCommandQueueExecuteCommandLists( return L0::CommandQueue::fromHandle(hCommandQueue)->executeCommandLists(numCommandLists, phCommandLists, hFence, true, nullptr, nullptr); } -ze_result_t zeCommandQueueSynchronize( +ze_result_t ZE_APICALL zeCommandQueueSynchronize( ze_command_queue_handle_t hCommandQueue, uint64_t timeout) { return L0::CommandQueue::fromHandle(hCommandQueue)->synchronize(timeout); } -ze_result_t zeCommandQueueGetOrdinal( +ze_result_t ZE_APICALL zeCommandQueueGetOrdinal( ze_command_queue_handle_t hCommandQueue, uint32_t *pOrdinal) { return L0::CommandQueue::fromHandle(hCommandQueue)->getOrdinal(pOrdinal); } -ze_result_t zeCommandQueueGetIndex( +ze_result_t ZE_APICALL zeCommandQueueGetIndex( ze_command_queue_handle_t hCommandQueue, uint32_t *pIndex) { return L0::CommandQueue::fromHandle(hCommandQueue)->getIndex(pIndex); diff --git a/level_zero/api/core/ze_context_api_entrypoints.h b/level_zero/api/core/ze_context_api_entrypoints.h index 3b3dea07d9..77b4ab9ddb 100644 --- a/level_zero/api/core/ze_context_api_entrypoints.h +++ b/level_zero/api/core/ze_context_api_entrypoints.h @@ -13,14 +13,14 @@ #include namespace L0 { -ze_result_t zeContextCreate( +ze_result_t ZE_APICALL zeContextCreate( ze_driver_handle_t hDriver, const ze_context_desc_t *desc, ze_context_handle_t *phContext) { return L0::DriverHandle::fromHandle(hDriver)->createContext(desc, 0u, nullptr, phContext); } -ze_result_t zeContextCreateEx( +ze_result_t ZE_APICALL zeContextCreateEx( ze_driver_handle_t hDriver, const ze_context_desc_t *desc, uint32_t numDevices, @@ -29,15 +29,15 @@ ze_result_t zeContextCreateEx( return L0::DriverHandle::fromHandle(hDriver)->createContext(desc, numDevices, phDevices, phContext); } -ze_result_t zeContextDestroy(ze_context_handle_t hContext) { +ze_result_t ZE_APICALL zeContextDestroy(ze_context_handle_t hContext) { return L0::Context::fromHandle(hContext)->destroy(); } -ze_result_t zeContextGetStatus(ze_context_handle_t hContext) { +ze_result_t ZE_APICALL zeContextGetStatus(ze_context_handle_t hContext) { return L0::Context::fromHandle(hContext)->getStatus(); } -ze_result_t zeVirtualMemReserve( +ze_result_t ZE_APICALL zeVirtualMemReserve( ze_context_handle_t hContext, const void *pStart, size_t size, @@ -45,14 +45,14 @@ ze_result_t zeVirtualMemReserve( return L0::Context::fromHandle(hContext)->reserveVirtualMem(pStart, size, pptr); } -ze_result_t zeVirtualMemFree( +ze_result_t ZE_APICALL zeVirtualMemFree( ze_context_handle_t hContext, const void *ptr, size_t size) { return L0::Context::fromHandle(hContext)->freeVirtualMem(ptr, size); } -ze_result_t zeVirtualMemQueryPageSize( +ze_result_t ZE_APICALL zeVirtualMemQueryPageSize( ze_context_handle_t hContext, ze_device_handle_t hDevice, size_t size, @@ -60,7 +60,7 @@ ze_result_t zeVirtualMemQueryPageSize( return L0::Context::fromHandle(hContext)->queryVirtualMemPageSize(hDevice, size, pagesize); } -ze_result_t zePhysicalMemCreate( +ze_result_t ZE_APICALL zePhysicalMemCreate( ze_context_handle_t hContext, ze_device_handle_t hDevice, ze_physical_mem_desc_t *desc, @@ -68,13 +68,13 @@ ze_result_t zePhysicalMemCreate( return L0::Context::fromHandle(hContext)->createPhysicalMem(hDevice, desc, phPhysicalMemory); } -ze_result_t zePhysicalMemDestroy( +ze_result_t ZE_APICALL zePhysicalMemDestroy( ze_context_handle_t hContext, ze_physical_mem_handle_t hPhysicalMemory) { return L0::Context::fromHandle(hContext)->destroyPhysicalMem(hPhysicalMemory); } -ze_result_t zeVirtualMemMap( +ze_result_t ZE_APICALL zeVirtualMemMap( ze_context_handle_t hContext, const void *ptr, size_t size, @@ -84,14 +84,14 @@ ze_result_t zeVirtualMemMap( return L0::Context::fromHandle(hContext)->mapVirtualMem(ptr, size, hPhysicalMemory, offset, access); } -ze_result_t zeVirtualMemUnmap( +ze_result_t ZE_APICALL zeVirtualMemUnmap( ze_context_handle_t hContext, const void *ptr, size_t size) { return L0::Context::fromHandle(hContext)->unMapVirtualMem(ptr, size); } -ze_result_t zeVirtualMemSetAccessAttribute( +ze_result_t ZE_APICALL zeVirtualMemSetAccessAttribute( ze_context_handle_t hContext, const void *ptr, size_t size, @@ -99,7 +99,7 @@ ze_result_t zeVirtualMemSetAccessAttribute( return L0::Context::fromHandle(hContext)->setVirtualMemAccessAttribute(ptr, size, access); } -ze_result_t zeVirtualMemGetAccessAttribute( +ze_result_t ZE_APICALL zeVirtualMemGetAccessAttribute( ze_context_handle_t hContext, const void *ptr, size_t size, @@ -108,13 +108,13 @@ ze_result_t zeVirtualMemGetAccessAttribute( return L0::Context::fromHandle(hContext)->getVirtualMemAccessAttribute(ptr, size, access, outSize); } -ze_result_t zeContextSystemBarrier( +ze_result_t ZE_APICALL zeContextSystemBarrier( ze_context_handle_t hContext, ze_device_handle_t hDevice) { return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zeContextMakeMemoryResident( +ze_result_t ZE_APICALL zeContextMakeMemoryResident( ze_context_handle_t hContext, ze_device_handle_t hDevice, void *ptr, @@ -122,7 +122,7 @@ ze_result_t zeContextMakeMemoryResident( return L0::Context::fromHandle(hContext)->makeMemoryResident(hDevice, ptr, size); } -ze_result_t zeContextEvictMemory( +ze_result_t ZE_APICALL zeContextEvictMemory( ze_context_handle_t hContext, ze_device_handle_t hDevice, void *ptr, @@ -130,14 +130,14 @@ ze_result_t zeContextEvictMemory( return L0::Context::fromHandle(hContext)->evictMemory(hDevice, ptr, size); } -ze_result_t zeContextMakeImageResident( +ze_result_t ZE_APICALL zeContextMakeImageResident( ze_context_handle_t hContext, ze_device_handle_t hDevice, ze_image_handle_t hImage) { return L0::Context::fromHandle(hContext)->makeImageResident(hDevice, hImage); } -ze_result_t zeContextEvictImage( +ze_result_t ZE_APICALL zeContextEvictImage( ze_context_handle_t hContext, ze_device_handle_t hDevice, ze_image_handle_t hImage) { diff --git a/level_zero/api/core/ze_copy_api_entrypoints.h b/level_zero/api/core/ze_copy_api_entrypoints.h index acb170024e..5e2e329f32 100644 --- a/level_zero/api/core/ze_copy_api_entrypoints.h +++ b/level_zero/api/core/ze_copy_api_entrypoints.h @@ -16,7 +16,7 @@ #include "graph_captured_apis.h" namespace L0 { -ze_result_t zeCommandListAppendMemoryCopy( +ze_result_t ZE_APICALL zeCommandListAppendMemoryCopy( ze_command_list_handle_t hCommandList, void *dstptr, const void *srcptr, @@ -34,7 +34,7 @@ ze_result_t zeCommandListAppendMemoryCopy( return cmdList->appendMemoryCopy(dstptr, srcptr, size, hSignalEvent, numWaitEvents, phWaitEvents, memoryCopyParams); } -ze_result_t zeCommandListAppendMemoryFill( +ze_result_t ZE_APICALL zeCommandListAppendMemoryFill( ze_command_list_handle_t hCommandList, void *ptr, const void *pattern, @@ -56,7 +56,7 @@ ze_result_t zeCommandListAppendMemoryFill( return cmdList->appendMemoryFill(ptr, pattern, patternSize, size, hEvent, numWaitEvents, phWaitEvents, memoryCopyParams); } -ze_result_t zeCommandListAppendMemoryCopyRegion( +ze_result_t ZE_APICALL zeCommandListAppendMemoryCopyRegion( ze_command_list_handle_t hCommandList, void *dstptr, const ze_copy_region_t *dstRegion, @@ -79,7 +79,7 @@ ze_result_t zeCommandListAppendMemoryCopyRegion( return cmdList->appendMemoryCopyRegion(dstptr, dstRegion, dstPitch, dstSlicePitch, srcptr, srcRegion, srcPitch, srcSlicePitch, hEvent, numWaitEvents, phWaitEvents, memoryCopyParams); } -ze_result_t zeCommandListAppendImageCopy( +ze_result_t ZE_APICALL zeCommandListAppendImageCopy( ze_command_list_handle_t hCommandList, ze_image_handle_t hDstImage, ze_image_handle_t hSrcImage, @@ -96,7 +96,7 @@ ze_result_t zeCommandListAppendImageCopy( return cmdList->appendImageCopy(hDstImage, hSrcImage, hSignalEvent, numWaitEvents, phWaitEvents, memoryCopyParams); } -ze_result_t zeCommandListAppendImageCopyRegion( +ze_result_t ZE_APICALL zeCommandListAppendImageCopyRegion( ze_command_list_handle_t hCommandList, ze_image_handle_t hDstImage, ze_image_handle_t hSrcImage, @@ -115,7 +115,7 @@ ze_result_t zeCommandListAppendImageCopyRegion( return cmdList->appendImageCopyRegion(hDstImage, hSrcImage, pDstRegion, pSrcRegion, hSignalEvent, numWaitEvents, phWaitEvents, memoryCopyParams); } -ze_result_t zeCommandListAppendImageCopyToMemory( +ze_result_t ZE_APICALL zeCommandListAppendImageCopyToMemory( ze_command_list_handle_t hCommandList, void *dstptr, ze_image_handle_t hSrcImage, @@ -133,7 +133,7 @@ ze_result_t zeCommandListAppendImageCopyToMemory( return cmdList->appendImageCopyToMemory(dstptr, hSrcImage, pSrcRegion, hSignalEvent, numWaitEvents, phWaitEvents, memoryCopyParams); } -ze_result_t zeCommandListAppendImageCopyFromMemory( +ze_result_t ZE_APICALL zeCommandListAppendImageCopyFromMemory( ze_command_list_handle_t hCommandList, ze_image_handle_t hDstImage, const void *srcptr, @@ -151,7 +151,7 @@ ze_result_t zeCommandListAppendImageCopyFromMemory( return cmdList->appendImageCopyFromMemory(hDstImage, srcptr, pDstRegion, hSignalEvent, numWaitEvents, phWaitEvents, memoryCopyParams); } -ze_result_t zeCommandListAppendImageCopyToMemoryExt( +ze_result_t ZE_APICALL zeCommandListAppendImageCopyToMemoryExt( ze_command_list_handle_t hCommandList, void *dstptr, ze_image_handle_t hSrcImage, @@ -171,7 +171,7 @@ ze_result_t zeCommandListAppendImageCopyToMemoryExt( return cmdList->appendImageCopyToMemoryExt(dstptr, hSrcImage, pSrcRegion, destRowPitch, destSlicePitch, hSignalEvent, numWaitEvents, phWaitEvents, memoryCopyParams); } -ze_result_t zeCommandListAppendImageCopyFromMemoryExt( +ze_result_t ZE_APICALL zeCommandListAppendImageCopyFromMemoryExt( ze_command_list_handle_t hCommandList, ze_image_handle_t hDstImage, const void *srcptr, @@ -191,7 +191,7 @@ ze_result_t zeCommandListAppendImageCopyFromMemoryExt( return cmdList->appendImageCopyFromMemoryExt(hDstImage, srcptr, pDstRegion, srcRowPitch, srcSlicePitch, hSignalEvent, numWaitEvents, phWaitEvents, memoryCopyParams); } -ze_result_t zeCommandListAppendMemoryPrefetch( +ze_result_t ZE_APICALL zeCommandListAppendMemoryPrefetch( ze_command_list_handle_t hCommandList, const void *ptr, size_t size) { @@ -204,7 +204,7 @@ ze_result_t zeCommandListAppendMemoryPrefetch( return cmdList->appendMemoryPrefetch(ptr, size); } -ze_result_t zeCommandListAppendMemAdvise( +ze_result_t ZE_APICALL zeCommandListAppendMemAdvise( ze_command_list_handle_t hCommandList, ze_device_handle_t hDevice, const void *ptr, @@ -219,7 +219,7 @@ ze_result_t zeCommandListAppendMemAdvise( return cmdList->appendMemAdvise(hDevice, ptr, size, advice); } -ze_result_t zeCommandListAppendMemoryCopyFromContext( +ze_result_t ZE_APICALL zeCommandListAppendMemoryCopyFromContext( ze_command_list_handle_t hCommandList, void *dstptr, ze_context_handle_t hContextSrc, diff --git a/level_zero/api/core/ze_device_api_entrypoints.h b/level_zero/api/core/ze_device_api_entrypoints.h index a0cbba70e7..3f8d1c9fdc 100644 --- a/level_zero/api/core/ze_device_api_entrypoints.h +++ b/level_zero/api/core/ze_device_api_entrypoints.h @@ -14,111 +14,111 @@ #include namespace L0 { -ze_result_t zeDeviceGet( +ze_result_t ZE_APICALL zeDeviceGet( ze_driver_handle_t hDriver, uint32_t *pCount, ze_device_handle_t *phDevices) { return L0::DriverHandle::fromHandle(hDriver)->getDevice(pCount, phDevices); } -ze_result_t zeDeviceGetSubDevices( +ze_result_t ZE_APICALL zeDeviceGetSubDevices( ze_device_handle_t hDevice, uint32_t *pCount, ze_device_handle_t *phSubdevices) { return L0::Device::fromHandle(hDevice)->getSubDevices(pCount, phSubdevices); } -ze_result_t zeDeviceGetProperties( +ze_result_t ZE_APICALL zeDeviceGetProperties( ze_device_handle_t hDevice, ze_device_properties_t *pDeviceProperties) { return L0::Device::fromHandle(hDevice)->getProperties(pDeviceProperties); } -ze_result_t zeDeviceGetComputeProperties( +ze_result_t ZE_APICALL zeDeviceGetComputeProperties( ze_device_handle_t hDevice, ze_device_compute_properties_t *pComputeProperties) { return L0::Device::fromHandle(hDevice)->getComputeProperties(pComputeProperties); } -ze_result_t zeDeviceGetModuleProperties( +ze_result_t ZE_APICALL zeDeviceGetModuleProperties( ze_device_handle_t hDevice, ze_device_module_properties_t *pKernelProperties) { return L0::Device::fromHandle(hDevice)->getKernelProperties(pKernelProperties); } -ze_result_t zeDeviceGetMemoryProperties( +ze_result_t ZE_APICALL zeDeviceGetMemoryProperties( ze_device_handle_t hDevice, uint32_t *pCount, ze_device_memory_properties_t *pMemProperties) { return L0::Device::fromHandle(hDevice)->getMemoryProperties(pCount, pMemProperties); } -ze_result_t zeDeviceGetMemoryAccessProperties( +ze_result_t ZE_APICALL zeDeviceGetMemoryAccessProperties( ze_device_handle_t hDevice, ze_device_memory_access_properties_t *pMemAccessProperties) { return L0::Device::fromHandle(hDevice)->getMemoryAccessProperties(pMemAccessProperties); } -ze_result_t zeDeviceGetCacheProperties( +ze_result_t ZE_APICALL zeDeviceGetCacheProperties( ze_device_handle_t hDevice, uint32_t *pCount, ze_device_cache_properties_t *pCacheProperties) { return L0::Device::fromHandle(hDevice)->getCacheProperties(pCount, pCacheProperties); } -ze_result_t zeDeviceGetImageProperties( +ze_result_t ZE_APICALL zeDeviceGetImageProperties( ze_device_handle_t hDevice, ze_device_image_properties_t *pImageProperties) { return L0::Device::fromHandle(hDevice)->getDeviceImageProperties(pImageProperties); } -ze_result_t zeDeviceGetP2PProperties( +ze_result_t ZE_APICALL zeDeviceGetP2PProperties( ze_device_handle_t hDevice, ze_device_handle_t hPeerDevice, ze_device_p2p_properties_t *pP2PProperties) { return L0::Device::fromHandle(hDevice)->getP2PProperties(hPeerDevice, pP2PProperties); } -ze_result_t zeDeviceCanAccessPeer( +ze_result_t ZE_APICALL zeDeviceCanAccessPeer( ze_device_handle_t hDevice, ze_device_handle_t hPeerDevice, ze_bool_t *value) { return L0::Device::fromHandle(hDevice)->canAccessPeer(hPeerDevice, value); } -ze_result_t zeDeviceGetCommandQueueGroupProperties( +ze_result_t ZE_APICALL zeDeviceGetCommandQueueGroupProperties( ze_device_handle_t hDevice, uint32_t *pCount, ze_command_queue_group_properties_t *pCommandQueueGroupProperties) { return L0::Device::fromHandle(hDevice)->getCommandQueueGroupProperties(pCount, pCommandQueueGroupProperties); } -ze_result_t zeDeviceGetExternalMemoryProperties( +ze_result_t ZE_APICALL zeDeviceGetExternalMemoryProperties( ze_device_handle_t hDevice, ze_device_external_memory_properties_t *pExternalMemoryProperties) { return L0::Device::fromHandle(hDevice)->getExternalMemoryProperties(pExternalMemoryProperties); } -ze_result_t zeDeviceGetStatus( +ze_result_t ZE_APICALL zeDeviceGetStatus( ze_device_handle_t hDevice) { return L0::Device::fromHandle(hDevice)->getStatus(); } -ze_result_t zeDeviceGetGlobalTimestamps( +ze_result_t ZE_APICALL zeDeviceGetGlobalTimestamps( ze_device_handle_t hDevice, uint64_t *hostTimestamp, uint64_t *deviceTimestamp) { return L0::Device::fromHandle(hDevice)->getGlobalTimestamps(hostTimestamp, deviceTimestamp); } -ze_result_t zeDeviceReserveCacheExt( +ze_result_t ZE_APICALL zeDeviceReserveCacheExt( ze_device_handle_t hDevice, size_t cacheLevel, size_t cacheReservationSize) { return L0::Device::fromHandle(hDevice)->reserveCache(cacheLevel, cacheReservationSize); } -ze_result_t zeDeviceSetCacheAdviceExt( +ze_result_t ZE_APICALL zeDeviceSetCacheAdviceExt( ze_device_handle_t hDevice, void *ptr, size_t regionSize, @@ -126,38 +126,38 @@ ze_result_t zeDeviceSetCacheAdviceExt( return L0::Device::fromHandle(hDevice)->setCacheAdvice(ptr, regionSize, cacheRegion); } -ze_result_t zeDevicePciGetPropertiesExt( +ze_result_t ZE_APICALL zeDevicePciGetPropertiesExt( ze_device_handle_t hDevice, ze_pci_ext_properties_t *pPciProperties) { return L0::Device::fromHandle(hDevice)->getPciProperties(pPciProperties); } -ze_result_t zeDeviceGetRootDevice( +ze_result_t ZE_APICALL zeDeviceGetRootDevice( ze_device_handle_t hDevice, ze_device_handle_t *phRootDevice) { return L0::Device::fromHandle(hDevice)->getRootDevice(phRootDevice); } -ze_result_t zeDeviceImportExternalSemaphoreExt( +ze_result_t ZE_APICALL zeDeviceImportExternalSemaphoreExt( ze_device_handle_t hDevice, const ze_external_semaphore_ext_desc_t *desc, ze_external_semaphore_ext_handle_t *phSemaphore) { return L0::ExternalSemaphore::importExternalSemaphore(hDevice, desc, phSemaphore); } -ze_result_t zeDeviceReleaseExternalSemaphoreExt( +ze_result_t ZE_APICALL zeDeviceReleaseExternalSemaphoreExt( ze_external_semaphore_ext_handle_t hSemaphore) { return L0::ExternalSemaphoreImp::fromHandle(hSemaphore)->releaseExternalSemaphore(); } -ze_result_t zeDeviceGetVectorWidthPropertiesExt( +ze_result_t ZE_APICALL zeDeviceGetVectorWidthPropertiesExt( ze_device_handle_t hDevice, uint32_t *pCount, ze_device_vector_width_properties_ext_t *pVectorWidthProperties) { return L0::Device::fromHandle(hDevice)->getVectorWidthPropertiesExt(pCount, pVectorWidthProperties); } -ze_result_t zeDeviceSynchronize(ze_device_handle_t hDevice) { +ze_result_t ZE_APICALL zeDeviceSynchronize(ze_device_handle_t hDevice) { return L0::Device::fromHandle(hDevice)->synchronize(); } ze_result_t ZE_APICALL zeDeviceGetPriorityLevels( diff --git a/level_zero/api/core/ze_driver_api_entrypoints.h b/level_zero/api/core/ze_driver_api_entrypoints.h index aff23e7002..309a54bcf3 100644 --- a/level_zero/api/core/ze_driver_api_entrypoints.h +++ b/level_zero/api/core/ze_driver_api_entrypoints.h @@ -12,67 +12,67 @@ #include namespace L0 { -ze_result_t zeInit( +ze_result_t ZE_APICALL zeInit( ze_init_flags_t flags) { return L0::init(flags); } -ze_result_t zeInitDrivers( +ze_result_t ZE_APICALL zeInitDrivers( uint32_t *pCount, ze_driver_handle_t *phDrivers, ze_init_driver_type_desc_t *desc) { return L0::initDrivers(pCount, phDrivers, desc); } -ze_result_t zeDriverGet( +ze_result_t ZE_APICALL zeDriverGet( uint32_t *pCount, ze_driver_handle_t *phDrivers) { return L0::Driver::get()->driverHandleGet(pCount, phDrivers); } -ze_result_t zeDriverGetProperties( +ze_result_t ZE_APICALL zeDriverGetProperties( ze_driver_handle_t hDriver, ze_driver_properties_t *pProperties) { return L0::DriverHandle::fromHandle(hDriver)->getProperties(pProperties); } -ze_result_t zeDriverGetApiVersion( +ze_result_t ZE_APICALL zeDriverGetApiVersion( ze_driver_handle_t hDriver, ze_api_version_t *version) { return L0::DriverHandle::fromHandle(hDriver)->getApiVersion(version); } -ze_result_t zeDriverGetIpcProperties( +ze_result_t ZE_APICALL zeDriverGetIpcProperties( ze_driver_handle_t hDriver, ze_driver_ipc_properties_t *pIPCProperties) { return L0::DriverHandle::fromHandle(hDriver)->getIPCProperties(pIPCProperties); } -ze_result_t zeDriverGetLastErrorDescription( +ze_result_t ZE_APICALL zeDriverGetLastErrorDescription( ze_driver_handle_t hDriver, const char **ppString) { return L0::DriverHandle::fromHandle(hDriver)->getErrorDescription(ppString); } -ze_result_t zeDriverGetExtensionProperties( +ze_result_t ZE_APICALL zeDriverGetExtensionProperties( ze_driver_handle_t hDriver, uint32_t *pCount, ze_driver_extension_properties_t *pExtensionProperties) { return L0::DriverHandle::fromHandle(hDriver)->getExtensionProperties(pCount, pExtensionProperties); } -ze_result_t zeDriverGetExtensionFunctionAddress( +ze_result_t ZE_APICALL zeDriverGetExtensionFunctionAddress( ze_driver_handle_t hDriver, const char *name, void **ppFunctionAddress) { return L0::BaseDriver::fromHandle(hDriver)->getExtensionFunctionAddress(name, ppFunctionAddress); } -ze_result_t zeDriverRTASFormatCompatibilityCheckExt(ze_driver_handle_t hDriver, - ze_rtas_format_ext_t rtasFormatA, - ze_rtas_format_ext_t rtasFormatB) { +ze_result_t ZE_APICALL zeDriverRTASFormatCompatibilityCheckExt(ze_driver_handle_t hDriver, + ze_rtas_format_ext_t rtasFormatA, + ze_rtas_format_ext_t rtasFormatB) { return L0::DriverHandle::fromHandle(hDriver)->formatRTASCompatibilityCheckExt(rtasFormatA, rtasFormatB); } -ze_context_handle_t zeDriverGetDefaultContext( +ze_context_handle_t ZE_APICALL zeDriverGetDefaultContext( ze_driver_handle_t hDriver) { return L0::DriverHandle::fromHandle(hDriver)->getDefaultContext(); } diff --git a/level_zero/api/core/ze_event_api_entrypoints.h b/level_zero/api/core/ze_event_api_entrypoints.h index 631c85ebd2..6178912fda 100644 --- a/level_zero/api/core/ze_event_api_entrypoints.h +++ b/level_zero/api/core/ze_event_api_entrypoints.h @@ -13,7 +13,7 @@ #include "graph_captured_apis.h" namespace L0 { -ze_result_t zeEventPoolCreate( +ze_result_t ZE_APICALL zeEventPoolCreate( ze_context_handle_t hContext, const ze_event_pool_desc_t *desc, uint32_t numDevices, @@ -22,42 +22,42 @@ ze_result_t zeEventPoolCreate( return L0::Context::fromHandle(hContext)->createEventPool(desc, numDevices, phDevices, phEventPool); } -ze_result_t zeEventPoolDestroy( +ze_result_t ZE_APICALL zeEventPoolDestroy( ze_event_pool_handle_t hEventPool) { return L0::EventPool::fromHandle(hEventPool)->destroy(); } -ze_result_t zeEventCreate( +ze_result_t ZE_APICALL zeEventCreate( ze_event_pool_handle_t hEventPool, const ze_event_desc_t *desc, ze_event_handle_t *phEvent) { return L0::EventPool::fromHandle(hEventPool)->createEvent(desc, phEvent); } -ze_result_t zeEventDestroy( +ze_result_t ZE_APICALL zeEventDestroy( ze_event_handle_t hEvent) { return L0::Event::fromHandle(hEvent)->destroy(); } -ze_result_t zeEventPoolGetIpcHandle( +ze_result_t ZE_APICALL zeEventPoolGetIpcHandle( ze_event_pool_handle_t hEventPool, ze_ipc_event_pool_handle_t *phIpc) { return L0::EventPool::fromHandle(hEventPool)->getIpcHandle(phIpc); } -ze_result_t zeEventPoolOpenIpcHandle( +ze_result_t ZE_APICALL zeEventPoolOpenIpcHandle( ze_context_handle_t hContext, ze_ipc_event_pool_handle_t hIpc, ze_event_pool_handle_t *phEventPool) { return L0::Context::fromHandle(hContext)->openEventPoolIpcHandle(hIpc, phEventPool); } -ze_result_t zeEventPoolCloseIpcHandle( +ze_result_t ZE_APICALL zeEventPoolCloseIpcHandle( ze_event_pool_handle_t hEventPool) { return L0::EventPool::fromHandle(hEventPool)->closeIpcHandle(); } -ze_result_t zeCommandListAppendSignalEvent( +ze_result_t ZE_APICALL zeCommandListAppendSignalEvent( ze_command_list_handle_t hCommandList, ze_event_handle_t hEvent) { auto cmdList = L0::CommandList::fromHandle(hCommandList); @@ -69,7 +69,7 @@ ze_result_t zeCommandListAppendSignalEvent( return cmdList->appendSignalEvent(hEvent, false); } -ze_result_t zeCommandListAppendWaitOnEvents( +ze_result_t ZE_APICALL zeCommandListAppendWaitOnEvents( ze_command_list_handle_t hCommandList, uint32_t numEvents, ze_event_handle_t *phEvents) { @@ -82,23 +82,23 @@ ze_result_t zeCommandListAppendWaitOnEvents( return cmdList->appendWaitOnEvents(numEvents, phEvents, nullptr, false, true, true, false, false, false); } -ze_result_t zeEventHostSignal( +ze_result_t ZE_APICALL zeEventHostSignal( ze_event_handle_t hEvent) { return L0::Event::fromHandle(hEvent)->hostSignal(false); } -ze_result_t zeEventHostSynchronize( +ze_result_t ZE_APICALL zeEventHostSynchronize( ze_event_handle_t hEvent, uint64_t timeout) { return L0::Event::fromHandle(hEvent)->hostSynchronize(timeout); } -ze_result_t zeEventQueryStatus( +ze_result_t ZE_APICALL zeEventQueryStatus( ze_event_handle_t hEvent) { return L0::Event::fromHandle(hEvent)->queryStatus(); } -ze_result_t zeCommandListAppendEventReset( +ze_result_t ZE_APICALL zeCommandListAppendEventReset( ze_command_list_handle_t hCommandList, ze_event_handle_t hEvent) { auto cmdList = L0::CommandList::fromHandle(hCommandList); @@ -110,18 +110,18 @@ ze_result_t zeCommandListAppendEventReset( return cmdList->appendEventReset(hEvent); } -ze_result_t zeEventHostReset( +ze_result_t ZE_APICALL zeEventHostReset( ze_event_handle_t hEvent) { return L0::Event::fromHandle(hEvent)->reset(); } -ze_result_t zeEventQueryKernelTimestamp( +ze_result_t ZE_APICALL zeEventQueryKernelTimestamp( ze_event_handle_t hEvent, ze_kernel_timestamp_result_t *timestampType) { return L0::Event::fromHandle(hEvent)->queryKernelTimestamp(timestampType); } -ze_result_t zeEventQueryKernelTimestampsExt( +ze_result_t ZE_APICALL zeEventQueryKernelTimestampsExt( ze_event_handle_t hEvent, ze_device_handle_t hDevice, uint32_t *pCount, @@ -129,37 +129,37 @@ ze_result_t zeEventQueryKernelTimestampsExt( return L0::Event::fromHandle(hEvent)->queryKernelTimestampsExt(L0::Device::fromHandle(hDevice), pCount, pResults); } -ze_result_t zeEventPoolPutIpcHandle( +ze_result_t ZE_APICALL zeEventPoolPutIpcHandle( ze_context_handle_t hContext, ze_ipc_event_pool_handle_t hIpc) { return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zeEventPoolGetContextHandle( +ze_result_t ZE_APICALL zeEventPoolGetContextHandle( ze_event_pool_handle_t hEventPool, ze_context_handle_t *phContext) { return L0::EventPool::fromHandle(hEventPool)->getContextHandle(phContext); } -ze_result_t zeEventPoolGetFlags( +ze_result_t ZE_APICALL zeEventPoolGetFlags( ze_event_pool_handle_t hEventPool, ze_event_pool_flags_t *pFlags) { return L0::EventPool::fromHandle(hEventPool)->getFlags(pFlags); } -ze_result_t zeEventGetEventPool( +ze_result_t ZE_APICALL zeEventGetEventPool( ze_event_handle_t hEvent, ze_event_pool_handle_t *phEventPool) { return L0::Event::fromHandle(hEvent)->getEventPool(phEventPool); } -ze_result_t zeEventGetSignalScope( +ze_result_t ZE_APICALL zeEventGetSignalScope( ze_event_handle_t hEvent, ze_event_scope_flags_t *pSignalScope) { return L0::Event::fromHandle(hEvent)->getSignalScope(pSignalScope); } -ze_result_t zeEventGetWaitScope( +ze_result_t ZE_APICALL zeEventGetWaitScope( ze_event_handle_t hEvent, ze_event_scope_flags_t *pWaitScope) { return L0::Event::fromHandle(hEvent)->getWaitScope(pWaitScope); diff --git a/level_zero/api/core/ze_fence_api_entrypoints.h b/level_zero/api/core/ze_fence_api_entrypoints.h index a720c060c7..54d2ee27ff 100644 --- a/level_zero/api/core/ze_fence_api_entrypoints.h +++ b/level_zero/api/core/ze_fence_api_entrypoints.h @@ -1,5 +1,5 @@ /* - * Copyright (C) 2020-2022 Intel Corporation + * Copyright (C) 2020-2025 Intel Corporation * * SPDX-License-Identifier: MIT * @@ -11,30 +11,30 @@ #include namespace L0 { -ze_result_t zeFenceCreate( +ze_result_t ZE_APICALL zeFenceCreate( ze_command_queue_handle_t hCommandQueue, const ze_fence_desc_t *desc, ze_fence_handle_t *phFence) { return L0::CommandQueue::fromHandle(hCommandQueue)->createFence(desc, phFence); } -ze_result_t zeFenceDestroy( +ze_result_t ZE_APICALL zeFenceDestroy( ze_fence_handle_t hFence) { return L0::Fence::fromHandle(hFence)->destroy(); } -ze_result_t zeFenceHostSynchronize( +ze_result_t ZE_APICALL zeFenceHostSynchronize( ze_fence_handle_t hFence, uint64_t timeout) { return L0::Fence::fromHandle(hFence)->hostSynchronize(timeout); } -ze_result_t zeFenceQueryStatus( +ze_result_t ZE_APICALL zeFenceQueryStatus( ze_fence_handle_t hFence) { return L0::Fence::fromHandle(hFence)->queryStatus(); } -ze_result_t zeFenceReset( +ze_result_t ZE_APICALL zeFenceReset( ze_fence_handle_t hFence) { return L0::Fence::fromHandle(hFence)->reset(false); } diff --git a/level_zero/api/core/ze_image_api_entrypoints.h b/level_zero/api/core/ze_image_api_entrypoints.h index 80f34d6048..4d3cb58aca 100644 --- a/level_zero/api/core/ze_image_api_entrypoints.h +++ b/level_zero/api/core/ze_image_api_entrypoints.h @@ -1,5 +1,5 @@ /* - * Copyright (C) 2020-2022 Intel Corporation + * Copyright (C) 2020-2025 Intel Corporation * * SPDX-License-Identifier: MIT * @@ -11,14 +11,14 @@ #include namespace L0 { -ze_result_t zeImageGetProperties( +ze_result_t ZE_APICALL zeImageGetProperties( ze_device_handle_t hDevice, const ze_image_desc_t *desc, ze_image_properties_t *pImageProperties) { return L0::Device::fromHandle(hDevice)->imageGetProperties(desc, pImageProperties); } -ze_result_t zeImageCreate( +ze_result_t ZE_APICALL zeImageCreate( ze_context_handle_t hContext, ze_device_handle_t hDevice, const ze_image_desc_t *desc, @@ -26,7 +26,7 @@ ze_result_t zeImageCreate( return L0::Context::fromHandle(hContext)->createImage(hDevice, desc, phImage); } -ze_result_t zeImageDestroy( +ze_result_t ZE_APICALL zeImageDestroy( ze_image_handle_t hImage) { return L0::Image::fromHandle(hImage)->destroy(); } diff --git a/level_zero/api/core/ze_memory_api_entrypoints.h b/level_zero/api/core/ze_memory_api_entrypoints.h index c7a4774036..f80ee1866a 100644 --- a/level_zero/api/core/ze_memory_api_entrypoints.h +++ b/level_zero/api/core/ze_memory_api_entrypoints.h @@ -11,7 +11,7 @@ #include namespace L0 { -ze_result_t zeMemAllocShared( +ze_result_t ZE_APICALL zeMemAllocShared( ze_context_handle_t hContext, const ze_device_mem_alloc_desc_t *deviceDesc, const ze_host_mem_alloc_desc_t *hostDesc, @@ -22,7 +22,7 @@ ze_result_t zeMemAllocShared( return L0::Context::fromHandle(hContext)->allocSharedMem(hDevice, deviceDesc, hostDesc, size, alignment, pptr); } -ze_result_t zeMemAllocDevice( +ze_result_t ZE_APICALL zeMemAllocDevice( ze_context_handle_t hContext, const ze_device_mem_alloc_desc_t *deviceDesc, size_t size, @@ -32,7 +32,7 @@ ze_result_t zeMemAllocDevice( return L0::Context::fromHandle(hContext)->allocDeviceMem(hDevice, deviceDesc, size, alignment, pptr); } -ze_result_t zeMemAllocHost( +ze_result_t ZE_APICALL zeMemAllocHost( ze_context_handle_t hContext, const ze_host_mem_alloc_desc_t *hostDesc, size_t size, @@ -41,20 +41,20 @@ ze_result_t zeMemAllocHost( return L0::Context::fromHandle(hContext)->allocHostMem(hostDesc, size, alignment, pptr); } -ze_result_t zeMemFree( +ze_result_t ZE_APICALL zeMemFree( ze_context_handle_t hContext, void *ptr) { return L0::Context::fromHandle(hContext)->freeMem(ptr); } -ze_result_t zeMemFreeExt( +ze_result_t ZE_APICALL zeMemFreeExt( ze_context_handle_t hContext, const ze_memory_free_ext_desc_t *pMemFreeDesc, void *ptr) { return L0::Context::fromHandle(hContext)->freeMemExt(pMemFreeDesc, ptr); } -ze_result_t zeMemGetAllocProperties( +ze_result_t ZE_APICALL zeMemGetAllocProperties( ze_context_handle_t hContext, const void *ptr, ze_memory_allocation_properties_t *pMemAllocProperties, @@ -62,7 +62,7 @@ ze_result_t zeMemGetAllocProperties( return L0::Context::fromHandle(hContext)->getMemAllocProperties(ptr, pMemAllocProperties, phDevice); } -ze_result_t zeMemGetAddressRange( +ze_result_t ZE_APICALL zeMemGetAddressRange( ze_context_handle_t hContext, const void *ptr, void **pBase, @@ -70,20 +70,20 @@ ze_result_t zeMemGetAddressRange( return L0::Context::fromHandle(hContext)->getMemAddressRange(ptr, pBase, pSize); } -ze_result_t zeMemGetIpcHandle( +ze_result_t ZE_APICALL zeMemGetIpcHandle( ze_context_handle_t hContext, const void *ptr, ze_ipc_mem_handle_t *pIpcHandle) { return L0::Context::fromHandle(hContext)->getIpcMemHandle(ptr, pIpcHandle); } -ze_result_t zeMemPutIpcHandle( +ze_result_t ZE_APICALL zeMemPutIpcHandle( ze_context_handle_t hContext, ze_ipc_mem_handle_t ipcHandle) { return L0::Context::fromHandle(hContext)->putIpcMemHandle(ipcHandle); } -ze_result_t zeMemOpenIpcHandle( +ze_result_t ZE_APICALL zeMemOpenIpcHandle( ze_context_handle_t hContext, ze_device_handle_t hDevice, ze_ipc_mem_handle_t handle, @@ -92,17 +92,17 @@ ze_result_t zeMemOpenIpcHandle( return L0::Context::fromHandle(hContext)->openIpcMemHandle(hDevice, handle, flags, pptr); } -ze_result_t zeMemCloseIpcHandle( +ze_result_t ZE_APICALL zeMemCloseIpcHandle( ze_context_handle_t hContext, const void *ptr) { return L0::Context::fromHandle(hContext)->closeIpcMemHandle(ptr); } -ze_result_t zeMemGetIpcHandleFromFileDescriptorExp(ze_context_handle_t hContext, uint64_t handle, ze_ipc_mem_handle_t *pIpcHandle) { +ze_result_t ZE_APICALL zeMemGetIpcHandleFromFileDescriptorExp(ze_context_handle_t hContext, uint64_t handle, ze_ipc_mem_handle_t *pIpcHandle) { return L0::Context::fromHandle(hContext)->getIpcHandleFromFd(handle, pIpcHandle); } -ze_result_t zeMemGetFileDescriptorFromIpcHandleExp(ze_context_handle_t hContext, ze_ipc_mem_handle_t ipcHandle, uint64_t *pHandle) { +ze_result_t ZE_APICALL zeMemGetFileDescriptorFromIpcHandleExp(ze_context_handle_t hContext, ze_ipc_mem_handle_t ipcHandle, uint64_t *pHandle) { return L0::Context::fromHandle(hContext)->getFdFromIpcHandle(ipcHandle, pHandle); } diff --git a/level_zero/api/core/ze_module_api_entrypoints.h b/level_zero/api/core/ze_module_api_entrypoints.h index d5e37cdfe5..d80dce8f5c 100644 --- a/level_zero/api/core/ze_module_api_entrypoints.h +++ b/level_zero/api/core/ze_module_api_entrypoints.h @@ -17,7 +17,7 @@ #include "graph_captured_apis.h" namespace L0 { -ze_result_t zeModuleCreate( +ze_result_t ZE_APICALL zeModuleCreate( ze_context_handle_t hContext, ze_device_handle_t hDevice, const ze_module_desc_t *desc, @@ -26,31 +26,31 @@ ze_result_t zeModuleCreate( return L0::Context::fromHandle(hContext)->createModule(hDevice, desc, phModule, phBuildLog); } -ze_result_t zeModuleDestroy( +ze_result_t ZE_APICALL zeModuleDestroy( ze_module_handle_t hModule) { return L0::Module::fromHandle(hModule)->destroy(); } -ze_result_t zeModuleBuildLogDestroy( +ze_result_t ZE_APICALL zeModuleBuildLogDestroy( ze_module_build_log_handle_t hModuleBuildLog) { return L0::ModuleBuildLog::fromHandle(hModuleBuildLog)->destroy(); } -ze_result_t zeModuleBuildLogGetString( +ze_result_t ZE_APICALL zeModuleBuildLogGetString( ze_module_build_log_handle_t hModuleBuildLog, size_t *pSize, char *pBuildLog) { return L0::ModuleBuildLog::fromHandle(hModuleBuildLog)->getString(pSize, pBuildLog); } -ze_result_t zeModuleGetNativeBinary( +ze_result_t ZE_APICALL zeModuleGetNativeBinary( ze_module_handle_t hModule, size_t *pSize, uint8_t *pModuleNativeBinary) { return L0::Module::fromHandle(hModule)->getNativeBinary(pSize, pModuleNativeBinary); } -ze_result_t zeModuleGetGlobalPointer( +ze_result_t ZE_APICALL zeModuleGetGlobalPointer( ze_module_handle_t hModule, const char *pGlobalName, size_t *pSize, @@ -58,33 +58,33 @@ ze_result_t zeModuleGetGlobalPointer( return L0::Module::fromHandle(hModule)->getGlobalPointer(pGlobalName, pSize, pptr); } -ze_result_t zeModuleGetKernelNames( +ze_result_t ZE_APICALL zeModuleGetKernelNames( ze_module_handle_t hModule, uint32_t *pCount, const char **pNames) { return L0::Module::fromHandle(hModule)->getKernelNames(pCount, pNames); } -ze_result_t zeKernelCreate( +ze_result_t ZE_APICALL zeKernelCreate( ze_module_handle_t hModule, const ze_kernel_desc_t *desc, ze_kernel_handle_t *kernelHandle) { return L0::Module::fromHandle(hModule)->createKernel(desc, kernelHandle); } -ze_result_t zeKernelDestroy( +ze_result_t ZE_APICALL zeKernelDestroy( ze_kernel_handle_t hKernel) { return L0::Kernel::fromHandle(hKernel)->destroy(); } -ze_result_t zeModuleGetFunctionPointer( +ze_result_t ZE_APICALL zeModuleGetFunctionPointer( ze_module_handle_t hModule, const char *pKernelName, void **pfnFunction) { return L0::Module::fromHandle(hModule)->getFunctionPointer(pKernelName, pfnFunction); } -ze_result_t zeKernelSetGroupSize( +ze_result_t ZE_APICALL zeKernelSetGroupSize( ze_kernel_handle_t hKernel, uint32_t groupSizeX, uint32_t groupSizeY, @@ -92,7 +92,7 @@ ze_result_t zeKernelSetGroupSize( return L0::Kernel::fromHandle(hKernel)->setGroupSize(groupSizeX, groupSizeY, groupSizeZ); } -ze_result_t zeKernelSuggestGroupSize( +ze_result_t ZE_APICALL zeKernelSuggestGroupSize( ze_kernel_handle_t hKernel, uint32_t globalSizeX, uint32_t globalSizeY, @@ -103,14 +103,14 @@ ze_result_t zeKernelSuggestGroupSize( return L0::Kernel::fromHandle(hKernel)->suggestGroupSize(globalSizeX, globalSizeY, globalSizeZ, groupSizeX, groupSizeY, groupSizeZ); } -ze_result_t zeKernelSuggestMaxCooperativeGroupCount( +ze_result_t ZE_APICALL zeKernelSuggestMaxCooperativeGroupCount( ze_kernel_handle_t hKernel, uint32_t *totalGroupCount) { *totalGroupCount = L0::Kernel::fromHandle(hKernel)->suggestMaxCooperativeGroupCount(NEO::EngineGroupType::compute, false); return ZE_RESULT_SUCCESS; } -ze_result_t zeKernelSetArgumentValue( +ze_result_t ZE_APICALL zeKernelSetArgumentValue( ze_kernel_handle_t hKernel, uint32_t argIndex, size_t argSize, @@ -118,39 +118,39 @@ ze_result_t zeKernelSetArgumentValue( return L0::Kernel::fromHandle(hKernel)->setArgumentValue(argIndex, argSize, pArgValue); } -ze_result_t zeKernelSetIndirectAccess( +ze_result_t ZE_APICALL zeKernelSetIndirectAccess( ze_kernel_handle_t hKernel, ze_kernel_indirect_access_flags_t flags) { return L0::Kernel::fromHandle(hKernel)->setIndirectAccess(flags); } -ze_result_t zeKernelGetIndirectAccess( +ze_result_t ZE_APICALL zeKernelGetIndirectAccess( ze_kernel_handle_t hKernel, ze_kernel_indirect_access_flags_t *pFlags) { return L0::Kernel::fromHandle(hKernel)->getIndirectAccess(pFlags); } -ze_result_t zeKernelGetSourceAttributes( +ze_result_t ZE_APICALL zeKernelGetSourceAttributes( ze_kernel_handle_t hKernel, uint32_t *pSize, char **pString) { return L0::Kernel::fromHandle(hKernel)->getSourceAttributes(pSize, pString); } -ze_result_t zeKernelGetProperties( +ze_result_t ZE_APICALL zeKernelGetProperties( ze_kernel_handle_t hKernel, ze_kernel_properties_t *pKernelProperties) { return L0::Kernel::fromHandle(hKernel)->getProperties(pKernelProperties); } -ze_result_t zeKernelGetBinaryExp( +ze_result_t ZE_APICALL zeKernelGetBinaryExp( ze_kernel_handle_t hKernel, size_t *pSize, uint8_t *pKernelBinary) { return L0::Kernel::fromHandle(hKernel)->getKernelProgramBinary(pSize, reinterpret_cast(pKernelBinary)); } -ze_result_t zeCommandListAppendLaunchKernel( +ze_result_t ZE_APICALL zeCommandListAppendLaunchKernel( ze_command_list_handle_t hCommandList, ze_kernel_handle_t kernelHandle, const ze_group_count_t *launchKernelArgs, @@ -170,7 +170,7 @@ ze_result_t zeCommandListAppendLaunchKernel( return cmdList->appendLaunchKernel(kernelHandle, *launchKernelArgs, hSignalEvent, numWaitEvents, phWaitEvents, launchParams); } -ze_result_t zeCommandListAppendLaunchCooperativeKernel( +ze_result_t ZE_APICALL zeCommandListAppendLaunchCooperativeKernel( ze_command_list_handle_t hCommandList, ze_kernel_handle_t kernelHandle, const ze_group_count_t *launchKernelArgs, @@ -190,7 +190,7 @@ ze_result_t zeCommandListAppendLaunchCooperativeKernel( return L0::CommandList::fromHandle(hCommandList)->appendLaunchKernel(kernelHandle, *launchKernelArgs, hSignalEvent, numWaitEvents, phWaitEvents, launchParams); } -ze_result_t zeCommandListAppendLaunchKernelIndirect( +ze_result_t ZE_APICALL zeCommandListAppendLaunchKernelIndirect( ze_command_list_handle_t hCommandList, ze_kernel_handle_t kernelHandle, const ze_group_count_t *pLaunchArgumentsBuffer, @@ -207,7 +207,7 @@ ze_result_t zeCommandListAppendLaunchKernelIndirect( return L0::CommandList::fromHandle(hCommandList)->appendLaunchKernelIndirect(kernelHandle, *pLaunchArgumentsBuffer, hSignalEvent, numWaitEvents, phWaitEvents, false); } -ze_result_t zeCommandListAppendLaunchMultipleKernelsIndirect( +ze_result_t ZE_APICALL zeCommandListAppendLaunchMultipleKernelsIndirect( ze_command_list_handle_t hCommandList, uint32_t numKernels, ze_kernel_handle_t *kernelHandles, @@ -226,27 +226,27 @@ ze_result_t zeCommandListAppendLaunchMultipleKernelsIndirect( return L0::CommandList::fromHandle(hCommandList)->appendLaunchMultipleKernelsIndirect(numKernels, kernelHandles, pCountBuffer, pLaunchArgumentsBuffer, hSignalEvent, numWaitEvents, phWaitEvents, false); } -ze_result_t zeKernelGetName( +ze_result_t ZE_APICALL zeKernelGetName( ze_kernel_handle_t hKernel, size_t *pSize, char *pName) { return L0::Kernel::fromHandle(hKernel)->getKernelName(pSize, pName); } -ze_result_t zeModuleDynamicLink( +ze_result_t ZE_APICALL zeModuleDynamicLink( uint32_t numModules, ze_module_handle_t *phModules, ze_module_build_log_handle_t *phLinkLog) { return L0::Module::fromHandle(phModules[0])->performDynamicLink(numModules, phModules, phLinkLog); } -ze_result_t zeModuleGetProperties( +ze_result_t ZE_APICALL zeModuleGetProperties( ze_module_handle_t hModule, ze_module_properties_t *pModuleProperties) { return L0::Module::fromHandle(hModule)->getProperties(pModuleProperties); } -ze_result_t zeModuleInspectLinkageExt( +ze_result_t ZE_APICALL zeModuleInspectLinkageExt( ze_linkage_inspection_ext_desc_t *pInspectDesc, uint32_t numModules, ze_module_handle_t *phModules, @@ -254,19 +254,19 @@ ze_result_t zeModuleInspectLinkageExt( return L0::Module::fromHandle(phModules[0])->inspectLinkage(pInspectDesc, numModules, phModules, phLog); } -ze_result_t zeKernelSetCacheConfig( +ze_result_t ZE_APICALL zeKernelSetCacheConfig( ze_kernel_handle_t hKernel, ze_cache_config_flags_t flags) { return L0::Kernel::fromHandle(hKernel)->setCacheConfig(flags); } -ze_result_t zeKernelSchedulingHintExp( +ze_result_t ZE_APICALL zeKernelSchedulingHintExp( ze_kernel_handle_t hKernel, ze_scheduling_hint_exp_desc_t *pHint) { return L0::Kernel::fromHandle(hKernel)->setSchedulingHintExp(pHint); } -ze_result_t zeKernelGetAllocationPropertiesExp( +ze_result_t ZE_APICALL zeKernelGetAllocationPropertiesExp( ze_kernel_handle_t hKernel, uint32_t *pCount, ze_kernel_allocation_exp_properties_t *pAllocationProperties) { diff --git a/level_zero/api/core/ze_sampler_api_entrypoints.h b/level_zero/api/core/ze_sampler_api_entrypoints.h index 107ce9873a..02c254bdf4 100644 --- a/level_zero/api/core/ze_sampler_api_entrypoints.h +++ b/level_zero/api/core/ze_sampler_api_entrypoints.h @@ -1,5 +1,5 @@ /* - * Copyright (C) 2020-2022 Intel Corporation + * Copyright (C) 2020-2025 Intel Corporation * * SPDX-License-Identifier: MIT * @@ -12,7 +12,7 @@ #include namespace L0 { -ze_result_t zeSamplerCreate( +ze_result_t ZE_APICALL zeSamplerCreate( ze_context_handle_t hContext, ze_device_handle_t hDevice, const ze_sampler_desc_t *desc, @@ -20,7 +20,7 @@ ze_result_t zeSamplerCreate( return L0::Context::fromHandle(hContext)->createSampler(hDevice, desc, phSampler); } -ze_result_t zeSamplerDestroy( +ze_result_t ZE_APICALL zeSamplerDestroy( ze_sampler_handle_t hSampler) { return L0::Sampler::fromHandle(hSampler)->destroy(); } diff --git a/level_zero/api/runtime/ze_runtime_all_api_entrypoints.h b/level_zero/api/runtime/ze_runtime_all_api_entrypoints.h index cc2cd25111..5089659d49 100644 --- a/level_zero/api/runtime/ze_runtime_all_api_entrypoints.h +++ b/level_zero/api/runtime/ze_runtime_all_api_entrypoints.h @@ -14,15 +14,15 @@ #include namespace L0 { -ze_context_handle_t zerGetDefaultContext() { +ze_context_handle_t ZE_APICALL zerGetDefaultContext() { return L0::DriverHandle::fromHandle(L0::globalDriverHandles->front())->getDefaultContext(); } -ze_result_t zerGetLastErrorDescription(const char **ppString) { +ze_result_t ZE_APICALL zerGetLastErrorDescription(const char **ppString) { return L0::DriverHandle::fromHandle(L0::globalDriverHandles->front())->getErrorDescription(ppString); } -uint32_t zerTranslateDeviceHandleToIdentifier(ze_device_handle_t device) { +uint32_t ZE_APICALL zerTranslateDeviceHandleToIdentifier(ze_device_handle_t device) { if (!device) { auto driverHandle = static_cast(L0::globalDriverHandles->front()); driverHandle->setErrorDescription("Invalid device handle"); @@ -31,7 +31,7 @@ uint32_t zerTranslateDeviceHandleToIdentifier(ze_device_handle_t device) { return L0::Device::fromHandle(device)->getIdentifier(); } -ze_device_handle_t zerTranslateIdentifierToDeviceHandle(uint32_t identifier) { +ze_device_handle_t ZE_APICALL zerTranslateIdentifierToDeviceHandle(uint32_t identifier) { auto driverHandle = static_cast(L0::globalDriverHandles->front()); if (identifier >= driverHandle->devicesToExpose.size()) { driverHandle->setErrorDescription("Invalid device identifier"); diff --git a/level_zero/api/sysman/zes_sysman_api_entrypoints.h b/level_zero/api/sysman/zes_sysman_api_entrypoints.h index 2d03670b13..f78a245907 100644 --- a/level_zero/api/sysman/zes_sysman_api_entrypoints.h +++ b/level_zero/api/sysman/zes_sysman_api_entrypoints.h @@ -32,12 +32,12 @@ inline ze_result_t dispatchSysmanApi(LegacyInitFunc legacyInitFunc, SysmanOnlyIn namespace L0 { -ze_result_t zesInit( +ze_result_t ZE_APICALL zesInit( zes_init_flags_t flags) { return L0::Sysman::init(flags); } -ze_result_t zesDriverGet( +ze_result_t ZE_APICALL zesDriverGet( uint32_t *pCount, zes_driver_handle_t *phDrivers) { if (L0::Sysman::sysmanOnlyInit) { @@ -47,7 +47,7 @@ ze_result_t zesDriverGet( } } -ze_result_t zesDeviceGet( +ze_result_t ZE_APICALL zesDeviceGet( zes_driver_handle_t hDriver, uint32_t *pCount, zes_device_handle_t *phDevices) { @@ -58,7 +58,7 @@ ze_result_t zesDeviceGet( } } -ze_result_t zesDriverGetExtensionProperties( +ze_result_t ZE_APICALL zesDriverGetExtensionProperties( zes_driver_handle_t hDriver, uint32_t *pCount, zes_driver_extension_properties_t *pExtensionProperties) { @@ -69,7 +69,7 @@ ze_result_t zesDriverGetExtensionProperties( } } -ze_result_t zesDriverGetExtensionFunctionAddress( +ze_result_t ZE_APICALL zesDriverGetExtensionFunctionAddress( zes_driver_handle_t hDriver, const char *name, void **ppFunctionAddress) { @@ -80,7 +80,7 @@ ze_result_t zesDriverGetExtensionFunctionAddress( } } -ze_result_t zesDeviceGetProperties( +ze_result_t ZE_APICALL zesDeviceGetProperties( zes_device_handle_t hDevice, zes_device_properties_t *pProperties) { return L0::Sysman::dispatchSysmanApi( @@ -88,7 +88,7 @@ ze_result_t zesDeviceGetProperties( [&]() { return L0::Sysman::SysmanDevice::deviceGetProperties(hDevice, pProperties); }); } -ze_result_t zesDeviceGetState( +ze_result_t ZE_APICALL zesDeviceGetState( zes_device_handle_t hDevice, zes_device_state_t *pState) { return L0::Sysman::dispatchSysmanApi( @@ -96,7 +96,7 @@ ze_result_t zesDeviceGetState( [&]() { return L0::Sysman::SysmanDevice::deviceGetState(hDevice, pState); }); } -ze_result_t zesDeviceGetSubDevicePropertiesExp( +ze_result_t ZE_APICALL zesDeviceGetSubDevicePropertiesExp( zes_device_handle_t hDevice, uint32_t *pCount, zes_subdevice_exp_properties_t *pSubdeviceProps) { @@ -105,7 +105,7 @@ ze_result_t zesDeviceGetSubDevicePropertiesExp( [&]() { return L0::Sysman::SysmanDevice::deviceGetSubDeviceProperties(hDevice, pCount, pSubdeviceProps); }); } -ze_result_t zesDriverGetDeviceByUuidExp( +ze_result_t ZE_APICALL zesDriverGetDeviceByUuidExp( zes_driver_handle_t hDriver, zes_uuid_t uuid, zes_device_handle_t *phDevice, @@ -116,7 +116,7 @@ ze_result_t zesDriverGetDeviceByUuidExp( [&]() { return L0::Sysman::SysmanDriverHandle::fromHandle(hDriver)->getDeviceByUuid(uuid, phDevice, onSubdevice, subdeviceId); }); } -ze_result_t zesDeviceEnumSchedulers( +ze_result_t ZE_APICALL zesDeviceEnumSchedulers( zes_device_handle_t hDevice, uint32_t *pCount, zes_sched_handle_t *phScheduler) { @@ -125,7 +125,7 @@ ze_result_t zesDeviceEnumSchedulers( [&]() { return L0::Sysman::SysmanDevice::schedulerGet(hDevice, pCount, phScheduler); }); } -ze_result_t zesSchedulerGetProperties( +ze_result_t ZE_APICALL zesSchedulerGetProperties( zes_sched_handle_t hScheduler, zes_sched_properties_t *pProperties) { return L0::Sysman::dispatchSysmanApi( @@ -133,7 +133,7 @@ ze_result_t zesSchedulerGetProperties( [&]() { return L0::Sysman::Scheduler::fromHandle(hScheduler)->schedulerGetProperties(pProperties); }); } -ze_result_t zesSchedulerGetCurrentMode( +ze_result_t ZE_APICALL zesSchedulerGetCurrentMode( zes_sched_handle_t hScheduler, zes_sched_mode_t *pMode) { return L0::Sysman::dispatchSysmanApi( @@ -141,7 +141,7 @@ ze_result_t zesSchedulerGetCurrentMode( [&]() { return L0::Sysman::Scheduler::fromHandle(hScheduler)->getCurrentMode(pMode); }); } -ze_result_t zesSchedulerGetTimeoutModeProperties( +ze_result_t ZE_APICALL zesSchedulerGetTimeoutModeProperties( zes_sched_handle_t hScheduler, ze_bool_t getDefaults, zes_sched_timeout_properties_t *pConfig) { @@ -150,7 +150,7 @@ ze_result_t zesSchedulerGetTimeoutModeProperties( [&]() { return L0::Sysman::Scheduler::fromHandle(hScheduler)->getTimeoutModeProperties(getDefaults, pConfig); }); } -ze_result_t zesSchedulerGetTimesliceModeProperties( +ze_result_t ZE_APICALL zesSchedulerGetTimesliceModeProperties( zes_sched_handle_t hScheduler, ze_bool_t getDefaults, zes_sched_timeslice_properties_t *pConfig) { @@ -159,7 +159,7 @@ ze_result_t zesSchedulerGetTimesliceModeProperties( [&]() { return L0::Sysman::Scheduler::fromHandle(hScheduler)->getTimesliceModeProperties(getDefaults, pConfig); }); } -ze_result_t zesSchedulerSetTimeoutMode( +ze_result_t ZE_APICALL zesSchedulerSetTimeoutMode( zes_sched_handle_t hScheduler, zes_sched_timeout_properties_t *pProperties, ze_bool_t *pNeedReload) { @@ -168,7 +168,7 @@ ze_result_t zesSchedulerSetTimeoutMode( [&]() { return L0::Sysman::Scheduler::fromHandle(hScheduler)->setTimeoutMode(pProperties, pNeedReload); }); } -ze_result_t zesSchedulerSetTimesliceMode( +ze_result_t ZE_APICALL zesSchedulerSetTimesliceMode( zes_sched_handle_t hScheduler, zes_sched_timeslice_properties_t *pProperties, ze_bool_t *pNeedReload) { @@ -177,7 +177,7 @@ ze_result_t zesSchedulerSetTimesliceMode( [&]() { return L0::Sysman::Scheduler::fromHandle(hScheduler)->setTimesliceMode(pProperties, pNeedReload); }); } -ze_result_t zesSchedulerSetExclusiveMode( +ze_result_t ZE_APICALL zesSchedulerSetExclusiveMode( zes_sched_handle_t hScheduler, ze_bool_t *pNeedReload) { return L0::Sysman::dispatchSysmanApi( @@ -185,7 +185,7 @@ ze_result_t zesSchedulerSetExclusiveMode( [&]() { return L0::Sysman::Scheduler::fromHandle(hScheduler)->setExclusiveMode(pNeedReload); }); } -ze_result_t zesSchedulerSetComputeUnitDebugMode( +ze_result_t ZE_APICALL zesSchedulerSetComputeUnitDebugMode( zes_sched_handle_t hScheduler, ze_bool_t *pNeedReload) { return L0::Sysman::dispatchSysmanApi( @@ -193,7 +193,7 @@ ze_result_t zesSchedulerSetComputeUnitDebugMode( [&]() { return L0::Sysman::Scheduler::fromHandle(hScheduler)->setComputeUnitDebugMode(pNeedReload); }); } -ze_result_t zesDeviceProcessesGetState( +ze_result_t ZE_APICALL zesDeviceProcessesGetState( zes_device_handle_t hDevice, uint32_t *pCount, zes_process_state_t *pProcesses) { @@ -202,7 +202,7 @@ ze_result_t zesDeviceProcessesGetState( [&]() { return L0::Sysman::SysmanDevice::processesGetState(hDevice, pCount, pProcesses); }); } -ze_result_t zesDeviceReset( +ze_result_t ZE_APICALL zesDeviceReset( zes_device_handle_t hDevice, ze_bool_t force) { return L0::Sysman::dispatchSysmanApi( @@ -210,7 +210,7 @@ ze_result_t zesDeviceReset( [&]() { return L0::Sysman::SysmanDevice::deviceReset(hDevice, force); }); } -ze_result_t zesDevicePciGetProperties( +ze_result_t ZE_APICALL zesDevicePciGetProperties( zes_device_handle_t hDevice, zes_pci_properties_t *pProperties) { return L0::Sysman::dispatchSysmanApi( @@ -218,7 +218,7 @@ ze_result_t zesDevicePciGetProperties( [&]() { return L0::Sysman::SysmanDevice::pciGetProperties(hDevice, pProperties); }); } -ze_result_t zesDevicePciGetState( +ze_result_t ZE_APICALL zesDevicePciGetState( zes_device_handle_t hDevice, zes_pci_state_t *pState) { return L0::Sysman::dispatchSysmanApi( @@ -226,7 +226,7 @@ ze_result_t zesDevicePciGetState( [&]() { return L0::Sysman::SysmanDevice::pciGetState(hDevice, pState); }); } -ze_result_t zesDevicePciGetBars( +ze_result_t ZE_APICALL zesDevicePciGetBars( zes_device_handle_t hDevice, uint32_t *pCount, zes_pci_bar_properties_t *pProperties) { @@ -235,7 +235,7 @@ ze_result_t zesDevicePciGetBars( [&]() { return L0::Sysman::SysmanDevice::pciGetBars(hDevice, pCount, pProperties); }); } -ze_result_t zesDevicePciGetStats( +ze_result_t ZE_APICALL zesDevicePciGetStats( zes_device_handle_t hDevice, zes_pci_stats_t *pStats) { return L0::Sysman::dispatchSysmanApi( @@ -243,7 +243,7 @@ ze_result_t zesDevicePciGetStats( [&]() { return L0::Sysman::SysmanDevice::pciGetStats(hDevice, pStats); }); } -ze_result_t zesDeviceEnumPowerDomains( +ze_result_t ZE_APICALL zesDeviceEnumPowerDomains( zes_device_handle_t hDevice, uint32_t *pCount, zes_pwr_handle_t *phPower) { @@ -252,7 +252,7 @@ ze_result_t zesDeviceEnumPowerDomains( [&]() { return L0::Sysman::SysmanDevice::powerGet(hDevice, pCount, phPower); }); } -ze_result_t zesDeviceGetCardPowerDomain( +ze_result_t ZE_APICALL zesDeviceGetCardPowerDomain( zes_device_handle_t hDevice, zes_pwr_handle_t *phPower) { return L0::Sysman::dispatchSysmanApi( @@ -260,7 +260,7 @@ ze_result_t zesDeviceGetCardPowerDomain( [&]() { return L0::Sysman::SysmanDevice::powerGetCardDomain(hDevice, phPower); }); } -ze_result_t zesPowerGetProperties( +ze_result_t ZE_APICALL zesPowerGetProperties( zes_pwr_handle_t hPower, zes_power_properties_t *pProperties) { return L0::Sysman::dispatchSysmanApi( @@ -268,7 +268,7 @@ ze_result_t zesPowerGetProperties( [&]() { return L0::Sysman::Power::fromHandle(hPower)->powerGetProperties(pProperties); }); } -ze_result_t zesPowerGetEnergyCounter( +ze_result_t ZE_APICALL zesPowerGetEnergyCounter( zes_pwr_handle_t hPower, zes_power_energy_counter_t *pEnergy) { return L0::Sysman::dispatchSysmanApi( @@ -276,7 +276,7 @@ ze_result_t zesPowerGetEnergyCounter( [&]() { return L0::Sysman::Power::fromHandle(hPower)->powerGetEnergyCounter(pEnergy); }); } -ze_result_t zesPowerGetLimits( +ze_result_t ZE_APICALL zesPowerGetLimits( zes_pwr_handle_t hPower, zes_power_sustained_limit_t *pSustained, zes_power_burst_limit_t *pBurst, @@ -286,7 +286,7 @@ ze_result_t zesPowerGetLimits( [&]() { return L0::Sysman::Power::fromHandle(hPower)->powerGetLimits(pSustained, pBurst, pPeak); }); } -ze_result_t zesPowerSetLimits( +ze_result_t ZE_APICALL zesPowerSetLimits( zes_pwr_handle_t hPower, const zes_power_sustained_limit_t *pSustained, const zes_power_burst_limit_t *pBurst, @@ -296,7 +296,7 @@ ze_result_t zesPowerSetLimits( [&]() { return L0::Sysman::Power::fromHandle(hPower)->powerSetLimits(pSustained, pBurst, pPeak); }); } -ze_result_t zesPowerGetLimitsExt( +ze_result_t ZE_APICALL zesPowerGetLimitsExt( zes_pwr_handle_t hPower, uint32_t *pCount, zes_power_limit_ext_desc_t *pSustained) { @@ -305,7 +305,7 @@ ze_result_t zesPowerGetLimitsExt( [&]() { return L0::Sysman::Power::fromHandle(hPower)->powerGetLimitsExt(pCount, pSustained); }); } -ze_result_t zesPowerSetLimitsExt( +ze_result_t ZE_APICALL zesPowerSetLimitsExt( zes_pwr_handle_t hPower, uint32_t *pCount, zes_power_limit_ext_desc_t *pSustained) { @@ -314,7 +314,7 @@ ze_result_t zesPowerSetLimitsExt( [&]() { return L0::Sysman::Power::fromHandle(hPower)->powerSetLimitsExt(pCount, pSustained); }); } -ze_result_t zesPowerGetEnergyThreshold( +ze_result_t ZE_APICALL zesPowerGetEnergyThreshold( zes_pwr_handle_t hPower, zes_energy_threshold_t *pThreshold) { return L0::Sysman::dispatchSysmanApi( @@ -322,7 +322,7 @@ ze_result_t zesPowerGetEnergyThreshold( [&]() { return L0::Sysman::Power::fromHandle(hPower)->powerGetEnergyThreshold(pThreshold); }); } -ze_result_t zesPowerSetEnergyThreshold( +ze_result_t ZE_APICALL zesPowerSetEnergyThreshold( zes_pwr_handle_t hPower, double threshold) { return L0::Sysman::dispatchSysmanApi( @@ -330,7 +330,7 @@ ze_result_t zesPowerSetEnergyThreshold( [&]() { return L0::Sysman::Power::fromHandle(hPower)->powerSetEnergyThreshold(threshold); }); } -ze_result_t zesDeviceEnumFrequencyDomains( +ze_result_t ZE_APICALL zesDeviceEnumFrequencyDomains( zes_device_handle_t hDevice, uint32_t *pCount, zes_freq_handle_t *phFrequency) { @@ -339,7 +339,7 @@ ze_result_t zesDeviceEnumFrequencyDomains( [&]() { return L0::Sysman::SysmanDevice::frequencyGet(hDevice, pCount, phFrequency); }); } -ze_result_t zesFrequencyGetProperties( +ze_result_t ZE_APICALL zesFrequencyGetProperties( zes_freq_handle_t hFrequency, zes_freq_properties_t *pProperties) { return L0::Sysman::dispatchSysmanApi( @@ -347,7 +347,7 @@ ze_result_t zesFrequencyGetProperties( [&]() { return L0::Sysman::Frequency::fromHandle(hFrequency)->frequencyGetProperties(pProperties); }); } -ze_result_t zesFrequencyGetAvailableClocks( +ze_result_t ZE_APICALL zesFrequencyGetAvailableClocks( zes_freq_handle_t hFrequency, uint32_t *pCount, double *phFrequency) { @@ -356,7 +356,7 @@ ze_result_t zesFrequencyGetAvailableClocks( [&]() { return L0::Sysman::Frequency::fromHandle(hFrequency)->frequencyGetAvailableClocks(pCount, phFrequency); }); } -ze_result_t zesFrequencyGetRange( +ze_result_t ZE_APICALL zesFrequencyGetRange( zes_freq_handle_t hFrequency, zes_freq_range_t *pLimits) { return L0::Sysman::dispatchSysmanApi( @@ -364,7 +364,7 @@ ze_result_t zesFrequencyGetRange( [&]() { return L0::Sysman::Frequency::fromHandle(hFrequency)->frequencyGetRange(pLimits); }); } -ze_result_t zesFrequencySetRange( +ze_result_t ZE_APICALL zesFrequencySetRange( zes_freq_handle_t hFrequency, const zes_freq_range_t *pLimits) { return L0::Sysman::dispatchSysmanApi( @@ -372,7 +372,7 @@ ze_result_t zesFrequencySetRange( [&]() { return L0::Sysman::Frequency::fromHandle(hFrequency)->frequencySetRange(pLimits); }); } -ze_result_t zesFrequencyGetState( +ze_result_t ZE_APICALL zesFrequencyGetState( zes_freq_handle_t hFrequency, zes_freq_state_t *pState) { return L0::Sysman::dispatchSysmanApi( @@ -380,7 +380,7 @@ ze_result_t zesFrequencyGetState( [&]() { return L0::Sysman::Frequency::fromHandle(hFrequency)->frequencyGetState(pState); }); } -ze_result_t zesFrequencyGetThrottleTime( +ze_result_t ZE_APICALL zesFrequencyGetThrottleTime( zes_freq_handle_t hFrequency, zes_freq_throttle_time_t *pThrottleTime) { return L0::Sysman::dispatchSysmanApi( @@ -388,7 +388,7 @@ ze_result_t zesFrequencyGetThrottleTime( [&]() { return L0::Sysman::Frequency::fromHandle(hFrequency)->frequencyGetThrottleTime(pThrottleTime); }); } -ze_result_t zesFrequencyOcGetFrequencyTarget( +ze_result_t ZE_APICALL zesFrequencyOcGetFrequencyTarget( zes_freq_handle_t hFrequency, double *pCurrentOcFrequency) { return L0::Sysman::dispatchSysmanApi( @@ -396,7 +396,7 @@ ze_result_t zesFrequencyOcGetFrequencyTarget( [&]() { return L0::Sysman::Frequency::fromHandle(hFrequency)->frequencyOcGetFrequencyTarget(pCurrentOcFrequency); }); } -ze_result_t zesFrequencyOcSetFrequencyTarget( +ze_result_t ZE_APICALL zesFrequencyOcSetFrequencyTarget( zes_freq_handle_t hFrequency, double currentOcFrequency) { return L0::Sysman::dispatchSysmanApi( @@ -404,7 +404,7 @@ ze_result_t zesFrequencyOcSetFrequencyTarget( [&]() { return L0::Sysman::Frequency::fromHandle(hFrequency)->frequencyOcSetFrequencyTarget(currentOcFrequency); }); } -ze_result_t zesFrequencyOcGetVoltageTarget( +ze_result_t ZE_APICALL zesFrequencyOcGetVoltageTarget( zes_freq_handle_t hFrequency, double *pCurrentVoltageTarget, double *pCurrentVoltageOffset) { @@ -413,7 +413,7 @@ ze_result_t zesFrequencyOcGetVoltageTarget( [&]() { return L0::Sysman::Frequency::fromHandle(hFrequency)->frequencyOcGetVoltageTarget(pCurrentVoltageTarget, pCurrentVoltageOffset); }); } -ze_result_t zesFrequencyOcSetVoltageTarget( +ze_result_t ZE_APICALL zesFrequencyOcSetVoltageTarget( zes_freq_handle_t hFrequency, double currentVoltageTarget, double currentVoltageOffset) { @@ -422,7 +422,7 @@ ze_result_t zesFrequencyOcSetVoltageTarget( [&]() { return L0::Sysman::Frequency::fromHandle(hFrequency)->frequencyOcSetVoltageTarget(currentVoltageTarget, currentVoltageOffset); }); } -ze_result_t zesFrequencyOcSetMode( +ze_result_t ZE_APICALL zesFrequencyOcSetMode( zes_freq_handle_t hFrequency, zes_oc_mode_t currentOcMode) { return L0::Sysman::dispatchSysmanApi( @@ -430,7 +430,7 @@ ze_result_t zesFrequencyOcSetMode( [&]() { return L0::Sysman::Frequency::fromHandle(hFrequency)->frequencyOcSetMode(currentOcMode); }); } -ze_result_t zesFrequencyOcGetMode( +ze_result_t ZE_APICALL zesFrequencyOcGetMode( zes_freq_handle_t hFrequency, zes_oc_mode_t *pCurrentOcMode) { return L0::Sysman::dispatchSysmanApi( @@ -438,7 +438,7 @@ ze_result_t zesFrequencyOcGetMode( [&]() { return L0::Sysman::Frequency::fromHandle(hFrequency)->frequencyOcGetMode(pCurrentOcMode); }); } -ze_result_t zesFrequencyOcGetCapabilities( +ze_result_t ZE_APICALL zesFrequencyOcGetCapabilities( zes_freq_handle_t hFrequency, zes_oc_capabilities_t *pOcCapabilities) { return L0::Sysman::dispatchSysmanApi( @@ -446,7 +446,7 @@ ze_result_t zesFrequencyOcGetCapabilities( [&]() { return L0::Sysman::Frequency::fromHandle(hFrequency)->frequencyOcGetCapabilities(pOcCapabilities); }); } -ze_result_t zesFrequencyOcGetIccMax( +ze_result_t ZE_APICALL zesFrequencyOcGetIccMax( zes_freq_handle_t hFrequency, double *pOcIccMax) { return L0::Sysman::dispatchSysmanApi( @@ -454,7 +454,7 @@ ze_result_t zesFrequencyOcGetIccMax( [&]() { return L0::Sysman::Frequency::fromHandle(hFrequency)->frequencyOcGetIccMax(pOcIccMax); }); } -ze_result_t zesFrequencyOcSetIccMax( +ze_result_t ZE_APICALL zesFrequencyOcSetIccMax( zes_freq_handle_t hFrequency, double ocIccMax) { return L0::Sysman::dispatchSysmanApi( @@ -462,7 +462,7 @@ ze_result_t zesFrequencyOcSetIccMax( [&]() { return L0::Sysman::Frequency::fromHandle(hFrequency)->frequencyOcSetIccMax(ocIccMax); }); } -ze_result_t zesFrequencyOcGetTjMax( +ze_result_t ZE_APICALL zesFrequencyOcGetTjMax( zes_freq_handle_t hFrequency, double *pOcTjMax) { return L0::Sysman::dispatchSysmanApi( @@ -470,7 +470,7 @@ ze_result_t zesFrequencyOcGetTjMax( [&]() { return L0::Sysman::Frequency::fromHandle(hFrequency)->frequencyOcGeTjMax(pOcTjMax); }); } -ze_result_t zesFrequencyOcSetTjMax( +ze_result_t ZE_APICALL zesFrequencyOcSetTjMax( zes_freq_handle_t hFrequency, double ocTjMax) { return L0::Sysman::dispatchSysmanApi( @@ -478,7 +478,7 @@ ze_result_t zesFrequencyOcSetTjMax( [&]() { return L0::Sysman::Frequency::fromHandle(hFrequency)->frequencyOcSetTjMax(ocTjMax); }); } -ze_result_t zesDeviceEnumEngineGroups( +ze_result_t ZE_APICALL zesDeviceEnumEngineGroups( zes_device_handle_t hDevice, uint32_t *pCount, zes_engine_handle_t *phEngine) { @@ -487,7 +487,7 @@ ze_result_t zesDeviceEnumEngineGroups( [&]() { return L0::Sysman::SysmanDevice::engineGet(hDevice, pCount, phEngine); }); } -ze_result_t zesEngineGetProperties( +ze_result_t ZE_APICALL zesEngineGetProperties( zes_engine_handle_t hEngine, zes_engine_properties_t *pProperties) { return L0::Sysman::dispatchSysmanApi( @@ -495,7 +495,7 @@ ze_result_t zesEngineGetProperties( [&]() { return L0::Sysman::Engine::fromHandle(hEngine)->engineGetProperties(pProperties); }); } -ze_result_t zesEngineGetActivity( +ze_result_t ZE_APICALL zesEngineGetActivity( zes_engine_handle_t hEngine, zes_engine_stats_t *pStats) { return L0::Sysman::dispatchSysmanApi( @@ -503,7 +503,7 @@ ze_result_t zesEngineGetActivity( [&]() { return L0::Sysman::Engine::fromHandle(hEngine)->engineGetActivity(pStats); }); } -ze_result_t zesDeviceEnumStandbyDomains( +ze_result_t ZE_APICALL zesDeviceEnumStandbyDomains( zes_device_handle_t hDevice, uint32_t *pCount, zes_standby_handle_t *phStandby) { @@ -512,7 +512,7 @@ ze_result_t zesDeviceEnumStandbyDomains( [&]() { return L0::Sysman::SysmanDevice::standbyGet(hDevice, pCount, phStandby); }); } -ze_result_t zesStandbyGetProperties( +ze_result_t ZE_APICALL zesStandbyGetProperties( zes_standby_handle_t hStandby, zes_standby_properties_t *pProperties) { return L0::Sysman::dispatchSysmanApi( @@ -520,7 +520,7 @@ ze_result_t zesStandbyGetProperties( [&]() { return L0::Sysman::Standby::fromHandle(hStandby)->standbyGetProperties(pProperties); }); } -ze_result_t zesStandbyGetMode( +ze_result_t ZE_APICALL zesStandbyGetMode( zes_standby_handle_t hStandby, zes_standby_promo_mode_t *pMode) { return L0::Sysman::dispatchSysmanApi( @@ -528,7 +528,7 @@ ze_result_t zesStandbyGetMode( [&]() { return L0::Sysman::Standby::fromHandle(hStandby)->standbyGetMode(pMode); }); } -ze_result_t zesStandbySetMode( +ze_result_t ZE_APICALL zesStandbySetMode( zes_standby_handle_t hStandby, zes_standby_promo_mode_t mode) { return L0::Sysman::dispatchSysmanApi( @@ -536,7 +536,7 @@ ze_result_t zesStandbySetMode( [&]() { return L0::Sysman::Standby::fromHandle(hStandby)->standbySetMode(mode); }); } -ze_result_t zesDeviceEnumFirmwares( +ze_result_t ZE_APICALL zesDeviceEnumFirmwares( zes_device_handle_t hDevice, uint32_t *pCount, zes_firmware_handle_t *phFirmware) { @@ -545,7 +545,7 @@ ze_result_t zesDeviceEnumFirmwares( [&]() { return L0::Sysman::SysmanDevice::firmwareGet(hDevice, pCount, phFirmware); }); } -ze_result_t zesFirmwareGetProperties( +ze_result_t ZE_APICALL zesFirmwareGetProperties( zes_firmware_handle_t hFirmware, zes_firmware_properties_t *pProperties) { return L0::Sysman::dispatchSysmanApi( @@ -553,7 +553,7 @@ ze_result_t zesFirmwareGetProperties( [&]() { return L0::Sysman::Firmware::fromHandle(hFirmware)->firmwareGetProperties(pProperties); }); } -ze_result_t zesFirmwareFlash( +ze_result_t ZE_APICALL zesFirmwareFlash( zes_firmware_handle_t hFirmware, void *pImage, uint32_t size) { @@ -562,7 +562,7 @@ ze_result_t zesFirmwareFlash( [&]() { return L0::Sysman::Firmware::fromHandle(hFirmware)->firmwareFlash(pImage, size); }); } -ze_result_t zesFirmwareGetFlashProgress( +ze_result_t ZE_APICALL zesFirmwareGetFlashProgress( zes_firmware_handle_t hFirmware, uint32_t *pCompletionPercent) { return L0::Sysman::dispatchSysmanApi( @@ -570,7 +570,7 @@ ze_result_t zesFirmwareGetFlashProgress( [&]() { return L0::Sysman::Firmware::fromHandle(hFirmware)->firmwareGetFlashProgress(pCompletionPercent); }); } -ze_result_t zesFirmwareGetSecurityVersionExp( +ze_result_t ZE_APICALL zesFirmwareGetSecurityVersionExp( zes_firmware_handle_t hFirmware, char *pVersion) { return L0::Sysman::dispatchSysmanApi( @@ -578,14 +578,14 @@ ze_result_t zesFirmwareGetSecurityVersionExp( [&]() { return L0::Sysman::Firmware::fromHandle(hFirmware)->firmwareGetSecurityVersion(pVersion); }); } -ze_result_t zesFirmwareSetSecurityVersionExp( +ze_result_t ZE_APICALL zesFirmwareSetSecurityVersionExp( zes_firmware_handle_t hFirmware) { return L0::Sysman::dispatchSysmanApi( [&]() { return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; }, [&]() { return L0::Sysman::Firmware::fromHandle(hFirmware)->firmwareSetSecurityVersion(); }); } -ze_result_t zesFirmwareGetConsoleLogs( +ze_result_t ZE_APICALL zesFirmwareGetConsoleLogs( zes_firmware_handle_t hFirmware, size_t *pSize, char *pFirmwareLog) { @@ -594,48 +594,48 @@ ze_result_t zesFirmwareGetConsoleLogs( [&]() { return L0::Sysman::Firmware::fromHandle(hFirmware)->firmwareGetConsoleLogs(pSize, pFirmwareLog); }); } -ze_result_t zesDeviceEnumActiveVFExp( +ze_result_t ZE_APICALL zesDeviceEnumActiveVFExp( zes_device_handle_t hDevice, uint32_t *pCount, zes_vf_handle_t *phVFhandle) { return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zesVFManagementGetVFPropertiesExp( +ze_result_t ZE_APICALL zesVFManagementGetVFPropertiesExp( zes_vf_handle_t hVFhandle, zes_vf_exp_properties_t *pProperties) { return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zesVFManagementGetVFMemoryUtilizationExp( +ze_result_t ZE_APICALL zesVFManagementGetVFMemoryUtilizationExp( zes_vf_handle_t hVFhandle, uint32_t *pCount, zes_vf_util_mem_exp_t *pMemUtil) { return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zesVFManagementGetVFEngineUtilizationExp( +ze_result_t ZE_APICALL zesVFManagementGetVFEngineUtilizationExp( zes_vf_handle_t hVFhandle, uint32_t *pCount, zes_vf_util_engine_exp_t *pEngineUtil) { return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zesVFManagementSetVFTelemetryModeExp( +ze_result_t ZE_APICALL zesVFManagementSetVFTelemetryModeExp( zes_vf_handle_t hVFhandle, zes_vf_info_util_exp_flags_t flags, ze_bool_t enable) { return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zesVFManagementSetVFTelemetrySamplingIntervalExp( +ze_result_t ZE_APICALL zesVFManagementSetVFTelemetrySamplingIntervalExp( zes_vf_handle_t hVFhandle, zes_vf_info_util_exp_flags_t flag, uint64_t samplingInterval) { return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zesDeviceEnumEnabledVFExp( +ze_result_t ZE_APICALL zesDeviceEnumEnabledVFExp( zes_device_handle_t hDevice, uint32_t *pCount, zes_vf_handle_t *phVFhandle) { @@ -644,13 +644,13 @@ ze_result_t zesDeviceEnumEnabledVFExp( [&]() { return L0::Sysman::SysmanDevice::deviceEnumEnabledVF(hDevice, pCount, phVFhandle); }); } -ze_result_t zesVFManagementGetVFCapabilitiesExp( +ze_result_t ZE_APICALL zesVFManagementGetVFCapabilitiesExp( zes_vf_handle_t hVFhandle, zes_vf_exp_capabilities_t *pCapability) { return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zesVFManagementGetVFMemoryUtilizationExp2( +ze_result_t ZE_APICALL zesVFManagementGetVFMemoryUtilizationExp2( zes_vf_handle_t hVFhandle, uint32_t *pCount, zes_vf_util_mem_exp2_t *pMemUtil) { @@ -659,7 +659,7 @@ ze_result_t zesVFManagementGetVFMemoryUtilizationExp2( [&]() { return L0::Sysman::VfManagement::fromHandle(hVFhandle)->vfGetMemoryUtilization(pCount, pMemUtil); }); } -ze_result_t zesVFManagementGetVFEngineUtilizationExp2( +ze_result_t ZE_APICALL zesVFManagementGetVFEngineUtilizationExp2( zes_vf_handle_t hVFhandle, uint32_t *pCount, zes_vf_util_engine_exp2_t *pEngineUtil) { @@ -668,7 +668,7 @@ ze_result_t zesVFManagementGetVFEngineUtilizationExp2( [&]() { return L0::Sysman::VfManagement::fromHandle(hVFhandle)->vfGetEngineUtilization(pCount, pEngineUtil); }); } -ze_result_t zesVFManagementGetVFCapabilitiesExp2( +ze_result_t ZE_APICALL zesVFManagementGetVFCapabilitiesExp2( zes_vf_handle_t hVFhandle, zes_vf_exp2_capabilities_t *pCapability) { return L0::Sysman::dispatchSysmanApi( @@ -676,7 +676,7 @@ ze_result_t zesVFManagementGetVFCapabilitiesExp2( [&]() { return L0::Sysman::VfManagement::fromHandle(hVFhandle)->vfGetCapabilities(pCapability); }); } -ze_result_t zesDeviceEnumMemoryModules( +ze_result_t ZE_APICALL zesDeviceEnumMemoryModules( zes_device_handle_t hDevice, uint32_t *pCount, zes_mem_handle_t *phMemory) { @@ -685,7 +685,7 @@ ze_result_t zesDeviceEnumMemoryModules( [&]() { return L0::Sysman::SysmanDevice::memoryGet(hDevice, pCount, phMemory); }); } -ze_result_t zesMemoryGetProperties( +ze_result_t ZE_APICALL zesMemoryGetProperties( zes_mem_handle_t hMemory, zes_mem_properties_t *pProperties) { return L0::Sysman::dispatchSysmanApi( @@ -693,7 +693,7 @@ ze_result_t zesMemoryGetProperties( [&]() { return L0::Sysman::Memory::fromHandle(hMemory)->memoryGetProperties(pProperties); }); } -ze_result_t zesMemoryGetState( +ze_result_t ZE_APICALL zesMemoryGetState( zes_mem_handle_t hMemory, zes_mem_state_t *pState) { return L0::Sysman::dispatchSysmanApi( @@ -701,7 +701,7 @@ ze_result_t zesMemoryGetState( [&]() { return L0::Sysman::Memory::fromHandle(hMemory)->memoryGetState(pState); }); } -ze_result_t zesMemoryGetBandwidth( +ze_result_t ZE_APICALL zesMemoryGetBandwidth( zes_mem_handle_t hMemory, zes_mem_bandwidth_t *pBandwidth) { return L0::Sysman::dispatchSysmanApi( @@ -709,7 +709,7 @@ ze_result_t zesMemoryGetBandwidth( [&]() { return L0::Sysman::Memory::fromHandle(hMemory)->memoryGetBandwidth(pBandwidth); }); } -ze_result_t zesDeviceEnumFabricPorts( +ze_result_t ZE_APICALL zesDeviceEnumFabricPorts( zes_device_handle_t hDevice, uint32_t *pCount, zes_fabric_port_handle_t *phPort) { @@ -718,7 +718,7 @@ ze_result_t zesDeviceEnumFabricPorts( [&]() { return L0::Sysman::SysmanDevice::fabricPortGet(hDevice, pCount, phPort); }); } -ze_result_t zesFabricPortGetProperties( +ze_result_t ZE_APICALL zesFabricPortGetProperties( zes_fabric_port_handle_t hPort, zes_fabric_port_properties_t *pProperties) { return L0::Sysman::dispatchSysmanApi( @@ -726,7 +726,7 @@ ze_result_t zesFabricPortGetProperties( [&]() { return L0::Sysman::FabricPort::fromHandle(hPort)->fabricPortGetProperties(pProperties); }); } -ze_result_t zesFabricPortGetLinkType( +ze_result_t ZE_APICALL zesFabricPortGetLinkType( zes_fabric_port_handle_t hPort, zes_fabric_link_type_t *pLinkType) { return L0::Sysman::dispatchSysmanApi( @@ -734,7 +734,7 @@ ze_result_t zesFabricPortGetLinkType( [&]() { return L0::Sysman::FabricPort::fromHandle(hPort)->fabricPortGetLinkType(pLinkType); }); } -ze_result_t zesFabricPortGetConfig( +ze_result_t ZE_APICALL zesFabricPortGetConfig( zes_fabric_port_handle_t hPort, zes_fabric_port_config_t *pConfig) { return L0::Sysman::dispatchSysmanApi( @@ -742,7 +742,7 @@ ze_result_t zesFabricPortGetConfig( [&]() { return L0::Sysman::FabricPort::fromHandle(hPort)->fabricPortGetConfig(pConfig); }); } -ze_result_t zesFabricPortSetConfig( +ze_result_t ZE_APICALL zesFabricPortSetConfig( zes_fabric_port_handle_t hPort, const zes_fabric_port_config_t *pConfig) { return L0::Sysman::dispatchSysmanApi( @@ -750,7 +750,7 @@ ze_result_t zesFabricPortSetConfig( [&]() { return L0::Sysman::FabricPort::fromHandle(hPort)->fabricPortSetConfig(pConfig); }); } -ze_result_t zesFabricPortGetState( +ze_result_t ZE_APICALL zesFabricPortGetState( zes_fabric_port_handle_t hPort, zes_fabric_port_state_t *pState) { return L0::Sysman::dispatchSysmanApi( @@ -758,7 +758,7 @@ ze_result_t zesFabricPortGetState( [&]() { return L0::Sysman::FabricPort::fromHandle(hPort)->fabricPortGetState(pState); }); } -ze_result_t zesFabricPortGetThroughput( +ze_result_t ZE_APICALL zesFabricPortGetThroughput( zes_fabric_port_handle_t hPort, zes_fabric_port_throughput_t *pThroughput) { return L0::Sysman::dispatchSysmanApi( @@ -766,7 +766,7 @@ ze_result_t zesFabricPortGetThroughput( [&]() { return L0::Sysman::FabricPort::fromHandle(hPort)->fabricPortGetThroughput(pThroughput); }); } -ze_result_t zesDeviceEnumTemperatureSensors( +ze_result_t ZE_APICALL zesDeviceEnumTemperatureSensors( zes_device_handle_t hDevice, uint32_t *pCount, zes_temp_handle_t *phTemperature) { @@ -775,7 +775,7 @@ ze_result_t zesDeviceEnumTemperatureSensors( [&]() { return L0::Sysman::SysmanDevice::temperatureGet(hDevice, pCount, phTemperature); }); } -ze_result_t zesTemperatureGetProperties( +ze_result_t ZE_APICALL zesTemperatureGetProperties( zes_temp_handle_t hTemperature, zes_temp_properties_t *pProperties) { return L0::Sysman::dispatchSysmanApi( @@ -783,7 +783,7 @@ ze_result_t zesTemperatureGetProperties( [&]() { return L0::Sysman::Temperature::fromHandle(hTemperature)->temperatureGetProperties(pProperties); }); } -ze_result_t zesTemperatureGetConfig( +ze_result_t ZE_APICALL zesTemperatureGetConfig( zes_temp_handle_t hTemperature, zes_temp_config_t *pConfig) { return L0::Sysman::dispatchSysmanApi( @@ -791,7 +791,7 @@ ze_result_t zesTemperatureGetConfig( [&]() { return L0::Sysman::Temperature::fromHandle(hTemperature)->temperatureGetConfig(pConfig); }); } -ze_result_t zesTemperatureSetConfig( +ze_result_t ZE_APICALL zesTemperatureSetConfig( zes_temp_handle_t hTemperature, const zes_temp_config_t *pConfig) { return L0::Sysman::dispatchSysmanApi( @@ -799,7 +799,7 @@ ze_result_t zesTemperatureSetConfig( [&]() { return L0::Sysman::Temperature::fromHandle(hTemperature)->temperatureSetConfig(pConfig); }); } -ze_result_t zesTemperatureGetState( +ze_result_t ZE_APICALL zesTemperatureGetState( zes_temp_handle_t hTemperature, double *pTemperature) { return L0::Sysman::dispatchSysmanApi( @@ -807,26 +807,26 @@ ze_result_t zesTemperatureGetState( [&]() { return L0::Sysman::Temperature::fromHandle(hTemperature)->temperatureGetState(pTemperature); }); } -ze_result_t zesDeviceEnumPsus( +ze_result_t ZE_APICALL zesDeviceEnumPsus( zes_device_handle_t hDevice, uint32_t *pCount, zes_psu_handle_t *phPsu) { return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zesPsuGetProperties( +ze_result_t ZE_APICALL zesPsuGetProperties( zes_psu_handle_t hPsu, zes_psu_properties_t *pProperties) { return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zesPsuGetState( +ze_result_t ZE_APICALL zesPsuGetState( zes_psu_handle_t hPsu, zes_psu_state_t *pState) { return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zesDeviceEnumFans( +ze_result_t ZE_APICALL zesDeviceEnumFans( zes_device_handle_t hDevice, uint32_t *pCount, zes_fan_handle_t *phFan) { @@ -835,7 +835,7 @@ ze_result_t zesDeviceEnumFans( [&]() { return L0::Sysman::SysmanDevice::fanGet(hDevice, pCount, phFan); }); } -ze_result_t zesFanGetProperties( +ze_result_t ZE_APICALL zesFanGetProperties( zes_fan_handle_t hFan, zes_fan_properties_t *pProperties) { return L0::Sysman::dispatchSysmanApi( @@ -843,7 +843,7 @@ ze_result_t zesFanGetProperties( [&]() { return L0::Sysman::Fan::fromHandle(hFan)->fanGetProperties(pProperties); }); } -ze_result_t zesFanGetConfig( +ze_result_t ZE_APICALL zesFanGetConfig( zes_fan_handle_t hFan, zes_fan_config_t *pConfig) { return L0::Sysman::dispatchSysmanApi( @@ -851,14 +851,14 @@ ze_result_t zesFanGetConfig( [&]() { return L0::Sysman::Fan::fromHandle(hFan)->fanGetConfig(pConfig); }); } -ze_result_t zesFanSetDefaultMode( +ze_result_t ZE_APICALL zesFanSetDefaultMode( zes_fan_handle_t hFan) { return L0::Sysman::dispatchSysmanApi( [&]() { return L0::Fan::fromHandle(hFan)->fanSetDefaultMode(); }, [&]() { return L0::Sysman::Fan::fromHandle(hFan)->fanSetDefaultMode(); }); } -ze_result_t zesFanSetFixedSpeedMode( +ze_result_t ZE_APICALL zesFanSetFixedSpeedMode( zes_fan_handle_t hFan, const zes_fan_speed_t *speed) { return L0::Sysman::dispatchSysmanApi( @@ -866,7 +866,7 @@ ze_result_t zesFanSetFixedSpeedMode( [&]() { return L0::Sysman::Fan::fromHandle(hFan)->fanSetFixedSpeedMode(speed); }); } -ze_result_t zesFanSetSpeedTableMode( +ze_result_t ZE_APICALL zesFanSetSpeedTableMode( zes_fan_handle_t hFan, const zes_fan_speed_table_t *speedTable) { return L0::Sysman::dispatchSysmanApi( @@ -874,7 +874,7 @@ ze_result_t zesFanSetSpeedTableMode( [&]() { return L0::Sysman::Fan::fromHandle(hFan)->fanSetSpeedTableMode(speedTable); }); } -ze_result_t zesFanGetState( +ze_result_t ZE_APICALL zesFanGetState( zes_fan_handle_t hFan, zes_fan_speed_units_t units, int32_t *pSpeed) { @@ -883,38 +883,38 @@ ze_result_t zesFanGetState( [&]() { return L0::Sysman::Fan::fromHandle(hFan)->fanGetState(units, pSpeed); }); } -ze_result_t zesDeviceEnumLeds( +ze_result_t ZE_APICALL zesDeviceEnumLeds( zes_device_handle_t hDevice, uint32_t *pCount, zes_led_handle_t *phLed) { return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zesLedGetProperties( +ze_result_t ZE_APICALL zesLedGetProperties( zes_led_handle_t hLed, zes_led_properties_t *pProperties) { return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zesLedGetState( +ze_result_t ZE_APICALL zesLedGetState( zes_led_handle_t hLed, zes_led_state_t *pState) { return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zesLedSetState( +ze_result_t ZE_APICALL zesLedSetState( zes_led_handle_t hLed, ze_bool_t enable) { return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zesLedSetColor( +ze_result_t ZE_APICALL zesLedSetColor( zes_led_handle_t hLed, const zes_led_color_t *pColor) { return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zesDeviceEnumRasErrorSets( +ze_result_t ZE_APICALL zesDeviceEnumRasErrorSets( zes_device_handle_t hDevice, uint32_t *pCount, zes_ras_handle_t *phRas) { @@ -923,7 +923,7 @@ ze_result_t zesDeviceEnumRasErrorSets( [&]() { return L0::Sysman::SysmanDevice::rasGet(hDevice, pCount, phRas); }); } -ze_result_t zesRasGetProperties( +ze_result_t ZE_APICALL zesRasGetProperties( zes_ras_handle_t hRas, zes_ras_properties_t *pProperties) { return L0::Sysman::dispatchSysmanApi( @@ -931,7 +931,7 @@ ze_result_t zesRasGetProperties( [&]() { return L0::Sysman::Ras::fromHandle(hRas)->rasGetProperties(pProperties); }); } -ze_result_t zesRasGetConfig( +ze_result_t ZE_APICALL zesRasGetConfig( zes_ras_handle_t hRas, zes_ras_config_t *pConfig) { return L0::Sysman::dispatchSysmanApi( @@ -939,7 +939,7 @@ ze_result_t zesRasGetConfig( [&]() { return L0::Sysman::Ras::fromHandle(hRas)->rasGetConfig(pConfig); }); } -ze_result_t zesRasSetConfig( +ze_result_t ZE_APICALL zesRasSetConfig( zes_ras_handle_t hRas, const zes_ras_config_t *pConfig) { return L0::Sysman::dispatchSysmanApi( @@ -947,7 +947,7 @@ ze_result_t zesRasSetConfig( [&]() { return L0::Sysman::Ras::fromHandle(hRas)->rasSetConfig(pConfig); }); } -ze_result_t zesRasGetState( +ze_result_t ZE_APICALL zesRasGetState( zes_ras_handle_t hRas, ze_bool_t clear, zes_ras_state_t *pState) { @@ -956,7 +956,7 @@ ze_result_t zesRasGetState( [&]() { return L0::Sysman::Ras::fromHandle(hRas)->rasGetState(pState, clear); }); } -ze_result_t zesRasGetStateExp( +ze_result_t ZE_APICALL zesRasGetStateExp( zes_ras_handle_t hRas, uint32_t *pCount, zes_ras_state_exp_t *pState) { @@ -965,7 +965,7 @@ ze_result_t zesRasGetStateExp( [&]() { return L0::Sysman::Ras::fromHandle(hRas)->rasGetStateExp(pCount, pState); }); } -ze_result_t zesRasClearStateExp( +ze_result_t ZE_APICALL zesRasClearStateExp( zes_ras_handle_t hRas, zes_ras_error_category_exp_t category) { return L0::Sysman::dispatchSysmanApi( @@ -973,7 +973,7 @@ ze_result_t zesRasClearStateExp( [&]() { return L0::Sysman::Ras::fromHandle(hRas)->rasClearStateExp(category); }); } -ze_result_t zesDeviceEventRegister( +ze_result_t ZE_APICALL zesDeviceEventRegister( zes_device_handle_t hDevice, zes_event_type_flags_t events) { return L0::Sysman::dispatchSysmanApi( @@ -981,7 +981,7 @@ ze_result_t zesDeviceEventRegister( [&]() { return L0::Sysman::SysmanDevice::deviceEventRegister(hDevice, events); }); } -ze_result_t zesDriverEventListen( +ze_result_t ZE_APICALL zesDriverEventListen( ze_driver_handle_t hDriver, uint32_t timeout, uint32_t count, @@ -993,7 +993,7 @@ ze_result_t zesDriverEventListen( [&]() { return L0::Sysman::SysmanDriverHandle::fromHandle(hDriver)->sysmanEventsListen(timeout, count, phDevices, pNumDeviceEvents, pEvents); }); } -ze_result_t zesDriverEventListenEx( +ze_result_t ZE_APICALL zesDriverEventListenEx( ze_driver_handle_t hDriver, uint64_t timeout, uint32_t count, @@ -1005,7 +1005,7 @@ ze_result_t zesDriverEventListenEx( [&]() { return L0::Sysman::SysmanDriverHandle::fromHandle(hDriver)->sysmanEventsListenEx(timeout, count, phDevices, pNumDeviceEvents, pEvents); }); } -ze_result_t zesDeviceEnumDiagnosticTestSuites( +ze_result_t ZE_APICALL zesDeviceEnumDiagnosticTestSuites( zes_device_handle_t hDevice, uint32_t *pCount, zes_diag_handle_t *phDiagnostics) { @@ -1014,7 +1014,7 @@ ze_result_t zesDeviceEnumDiagnosticTestSuites( [&]() { return L0::Sysman::SysmanDevice::diagnosticsGet(hDevice, pCount, phDiagnostics); }); } -ze_result_t zesDiagnosticsGetProperties( +ze_result_t ZE_APICALL zesDiagnosticsGetProperties( zes_diag_handle_t hDiagnostics, zes_diag_properties_t *pProperties) { return L0::Sysman::dispatchSysmanApi( @@ -1022,7 +1022,7 @@ ze_result_t zesDiagnosticsGetProperties( [&]() { return L0::Sysman::Diagnostics::fromHandle(hDiagnostics)->diagnosticsGetProperties(pProperties); }); } -ze_result_t zesDiagnosticsGetTests( +ze_result_t ZE_APICALL zesDiagnosticsGetTests( zes_diag_handle_t hDiagnostics, uint32_t *pCount, zes_diag_test_t *pTests) { @@ -1031,7 +1031,7 @@ ze_result_t zesDiagnosticsGetTests( [&]() { return L0::Sysman::Diagnostics::fromHandle(hDiagnostics)->diagnosticsGetTests(pCount, pTests); }); } -ze_result_t zesDiagnosticsRunTests( +ze_result_t ZE_APICALL zesDiagnosticsRunTests( zes_diag_handle_t hDiagnostics, uint32_t startIndex, uint32_t endIndex, @@ -1041,7 +1041,7 @@ ze_result_t zesDiagnosticsRunTests( [&]() { return L0::Sysman::Diagnostics::fromHandle(hDiagnostics)->diagnosticsRunTests(startIndex, endIndex, pResult); }); } -ze_result_t zesDeviceEnumPerformanceFactorDomains( +ze_result_t ZE_APICALL zesDeviceEnumPerformanceFactorDomains( zes_device_handle_t hDevice, uint32_t *pCount, zes_perf_handle_t *phPerf) { @@ -1050,7 +1050,7 @@ ze_result_t zesDeviceEnumPerformanceFactorDomains( [&]() { return L0::Sysman::SysmanDevice::performanceGet(hDevice, pCount, phPerf); }); } -ze_result_t zesPerformanceFactorGetProperties( +ze_result_t ZE_APICALL zesPerformanceFactorGetProperties( zes_perf_handle_t hPerf, zes_perf_properties_t *pProperties) { return L0::Sysman::dispatchSysmanApi( @@ -1058,7 +1058,7 @@ ze_result_t zesPerformanceFactorGetProperties( [&]() { return L0::Sysman::Performance::fromHandle(hPerf)->performanceGetProperties(pProperties); }); } -ze_result_t zesPerformanceFactorGetConfig( +ze_result_t ZE_APICALL zesPerformanceFactorGetConfig( zes_perf_handle_t hPerf, double *pFactor) { return L0::Sysman::dispatchSysmanApi( @@ -1066,7 +1066,7 @@ ze_result_t zesPerformanceFactorGetConfig( [&]() { return L0::Sysman::Performance::fromHandle(hPerf)->performanceGetConfig(pFactor); }); } -ze_result_t zesPerformanceFactorSetConfig( +ze_result_t ZE_APICALL zesPerformanceFactorSetConfig( zes_perf_handle_t hPerf, double factor) { return L0::Sysman::dispatchSysmanApi( @@ -1074,7 +1074,7 @@ ze_result_t zesPerformanceFactorSetConfig( [&]() { return L0::Sysman::Performance::fromHandle(hPerf)->performanceSetConfig(factor); }); } -ze_result_t zesDeviceEccAvailable( +ze_result_t ZE_APICALL zesDeviceEccAvailable( zes_device_handle_t hDevice, ze_bool_t *pAvailable) { return L0::Sysman::dispatchSysmanApi( @@ -1082,7 +1082,7 @@ ze_result_t zesDeviceEccAvailable( [&]() { return L0::Sysman::SysmanDevice::deviceEccAvailable(hDevice, pAvailable); }); } -ze_result_t zesDeviceEccConfigurable( +ze_result_t ZE_APICALL zesDeviceEccConfigurable( zes_device_handle_t hDevice, ze_bool_t *pConfigurable) { return L0::Sysman::dispatchSysmanApi( @@ -1090,7 +1090,7 @@ ze_result_t zesDeviceEccConfigurable( [&]() { return L0::Sysman::SysmanDevice::deviceEccConfigurable(hDevice, pConfigurable); }); } -ze_result_t zesDeviceGetEccState( +ze_result_t ZE_APICALL zesDeviceGetEccState( zes_device_handle_t hDevice, zes_device_ecc_properties_t *pState) { return L0::Sysman::dispatchSysmanApi( @@ -1098,7 +1098,7 @@ ze_result_t zesDeviceGetEccState( [&]() { return L0::Sysman::SysmanDevice::deviceGetEccState(hDevice, pState); }); } -ze_result_t zesDeviceSetEccState( +ze_result_t ZE_APICALL zesDeviceSetEccState( zes_device_handle_t hDevice, const zes_device_ecc_desc_t *newState, zes_device_ecc_properties_t *pState) { @@ -1107,40 +1107,40 @@ ze_result_t zesDeviceSetEccState( [&]() { return L0::Sysman::SysmanDevice::deviceSetEccState(hDevice, newState, pState); }); } -ze_result_t zesOverclockGetDomainProperties( +ze_result_t ZE_APICALL zesOverclockGetDomainProperties( zes_overclock_handle_t hDomainHandle, zes_overclock_properties_t *pDomainProperties) { return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zesOverclockGetDomainVFProperties( +ze_result_t ZE_APICALL zesOverclockGetDomainVFProperties( zes_overclock_handle_t hDomainHandle, zes_vf_property_t *pVFProperties) { return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zesOverclockGetDomainControlProperties( +ze_result_t ZE_APICALL zesOverclockGetDomainControlProperties( zes_overclock_handle_t hDomainHandle, zes_overclock_control_t domainControl, zes_control_property_t *pControlProperties) { return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zesOverclockGetControlCurrentValue( +ze_result_t ZE_APICALL zesOverclockGetControlCurrentValue( zes_overclock_handle_t hDomainHandle, zes_overclock_control_t domainControl, double *pValue) { return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zesOverclockGetControlPendingValue( +ze_result_t ZE_APICALL zesOverclockGetControlPendingValue( zes_overclock_handle_t hDomainHandle, zes_overclock_control_t domainControl, double *pValue) { return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zesOverclockSetControlUserValue( +ze_result_t ZE_APICALL zesOverclockSetControlUserValue( zes_overclock_handle_t hDomainHandle, zes_overclock_control_t domainControl, double pValue, @@ -1148,7 +1148,7 @@ ze_result_t zesOverclockSetControlUserValue( return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zesOverclockGetControlState( +ze_result_t ZE_APICALL zesOverclockGetControlState( zes_overclock_handle_t hDomainHandle, zes_overclock_control_t domainControl, zes_control_state_t *pControlState, @@ -1156,7 +1156,7 @@ ze_result_t zesOverclockGetControlState( return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zesOverclockGetVFPointValues( +ze_result_t ZE_APICALL zesOverclockGetVFPointValues( zes_overclock_handle_t hDomainHandle, zes_vf_type_t vfType, zes_vf_array_type_t vfArrayType, @@ -1165,7 +1165,7 @@ ze_result_t zesOverclockGetVFPointValues( return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zesOverclockSetVFPointValues( +ze_result_t ZE_APICALL zesOverclockSetVFPointValues( zes_overclock_handle_t hDomainHandle, zes_vf_type_t vfType, uint32_t pointIndex, @@ -1173,31 +1173,31 @@ ze_result_t zesOverclockSetVFPointValues( return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zesDeviceSetOverclockWaiver( +ze_result_t ZE_APICALL zesDeviceSetOverclockWaiver( zes_device_handle_t hDevice) { return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zesDeviceGetOverclockDomains( +ze_result_t ZE_APICALL zesDeviceGetOverclockDomains( zes_device_handle_t hDevice, uint32_t *pOverclockDomains) { return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zesDeviceGetOverclockControls( +ze_result_t ZE_APICALL zesDeviceGetOverclockControls( zes_device_handle_t hDevice, zes_overclock_domain_t domainType, uint32_t *pAvailableControls) { return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zesDeviceResetOverclockSettings( +ze_result_t ZE_APICALL zesDeviceResetOverclockSettings( zes_device_handle_t hDevice, ze_bool_t onShippedState) { return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zesDeviceReadOverclockState( +ze_result_t ZE_APICALL zesDeviceReadOverclockState( zes_device_handle_t hDevice, zes_overclock_mode_t *pOverclockMode, ze_bool_t *pWaiverSetting, @@ -1207,14 +1207,14 @@ ze_result_t zesDeviceReadOverclockState( return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zesDeviceEnumOverclockDomains( +ze_result_t ZE_APICALL zesDeviceEnumOverclockDomains( zes_device_handle_t hDevice, uint32_t *pCount, zes_overclock_handle_t *phDomainHandle) { return ZE_RESULT_ERROR_UNSUPPORTED_FEATURE; } -ze_result_t zesDeviceResetExt( +ze_result_t ZE_APICALL zesDeviceResetExt( zes_device_handle_t hDevice, zes_reset_properties_t *pProperties) { return L0::Sysman::dispatchSysmanApi( @@ -1222,7 +1222,7 @@ ze_result_t zesDeviceResetExt( [&]() { return L0::Sysman::SysmanDevice::deviceResetExt(hDevice, pProperties); }); } -ze_result_t zesEngineGetActivityExt( +ze_result_t ZE_APICALL zesEngineGetActivityExt( zes_engine_handle_t hEngine, uint32_t *pCount, zes_engine_stats_t *pStats) { @@ -1231,7 +1231,7 @@ ze_result_t zesEngineGetActivityExt( [&]() { return L0::Sysman::Engine::fromHandle(hEngine)->engineGetActivityExt(pCount, pStats); }); } -ze_result_t zesFabricPortGetFabricErrorCounters( +ze_result_t ZE_APICALL zesFabricPortGetFabricErrorCounters( zes_fabric_port_handle_t hPort, zes_fabric_port_error_counters_t *pErrors) { return L0::Sysman::dispatchSysmanApi( @@ -1239,7 +1239,7 @@ ze_result_t zesFabricPortGetFabricErrorCounters( [&]() { return L0::Sysman::FabricPort::fromHandle(hPort)->fabricPortGetErrorCounters(pErrors); }); } -ze_result_t zesFabricPortGetMultiPortThroughput( +ze_result_t ZE_APICALL zesFabricPortGetMultiPortThroughput( zes_device_handle_t hDevice, uint32_t numPorts, zes_fabric_port_handle_t *phPort, diff --git a/level_zero/api/tools/zet_debug_api_entrypoints.h b/level_zero/api/tools/zet_debug_api_entrypoints.h index fa16b6b811..da6810b787 100644 --- a/level_zero/api/tools/zet_debug_api_entrypoints.h +++ b/level_zero/api/tools/zet_debug_api_entrypoints.h @@ -1,5 +1,5 @@ /* - * Copyright (C) 2020-2023 Intel Corporation + * Copyright (C) 2020-2025 Intel Corporation * * SPDX-License-Identifier: MIT * @@ -12,44 +12,44 @@ #include namespace L0 { -ze_result_t zetDeviceGetDebugProperties( +ze_result_t ZE_APICALL zetDeviceGetDebugProperties( zet_device_handle_t hDevice, zet_device_debug_properties_t *pDebugProperties) { return L0::Device::fromHandle(hDevice)->getDebugProperties(pDebugProperties); } -ze_result_t zetDebugAttach( +ze_result_t ZE_APICALL zetDebugAttach( zet_device_handle_t hDevice, const zet_debug_config_t *config, zet_debug_session_handle_t *phDebug) { return L0::DebugApiHandlers::debugAttach(hDevice, config, phDebug); } -ze_result_t zetDebugDetach( +ze_result_t ZE_APICALL zetDebugDetach( zet_debug_session_handle_t hDebug) { return L0::DebugApiHandlers::debugDetach(hDebug); } -ze_result_t zetDebugReadEvent( +ze_result_t ZE_APICALL zetDebugReadEvent( zet_debug_session_handle_t hDebug, uint64_t timeout, zet_debug_event_t *event) { return L0::DebugApiHandlers::debugReadEvent(hDebug, timeout, event); } -ze_result_t zetDebugInterrupt( +ze_result_t ZE_APICALL zetDebugInterrupt( zet_debug_session_handle_t hDebug, ze_device_thread_t thread) { return L0::DebugApiHandlers::debugInterrupt(hDebug, thread); } -ze_result_t zetDebugResume( +ze_result_t ZE_APICALL zetDebugResume( zet_debug_session_handle_t hDebug, ze_device_thread_t thread) { return L0::DebugApiHandlers::debugResume(hDebug, thread); } -ze_result_t zetDebugReadMemory( +ze_result_t ZE_APICALL zetDebugReadMemory( zet_debug_session_handle_t hDebug, ze_device_thread_t thread, const zet_debug_memory_space_desc_t *desc, @@ -58,7 +58,7 @@ ze_result_t zetDebugReadMemory( return L0::DebugApiHandlers::debugReadMemory(hDebug, thread, desc, size, buffer); } -ze_result_t zetDebugWriteMemory( +ze_result_t ZE_APICALL zetDebugWriteMemory( zet_debug_session_handle_t hDebug, ze_device_thread_t thread, const zet_debug_memory_space_desc_t *desc, @@ -67,20 +67,20 @@ ze_result_t zetDebugWriteMemory( return L0::DebugApiHandlers::debugWriteMemory(hDebug, thread, desc, size, buffer); } -ze_result_t zetDebugAcknowledgeEvent( +ze_result_t ZE_APICALL zetDebugAcknowledgeEvent( zet_debug_session_handle_t hDebug, const zet_debug_event_t *event) { return L0::DebugApiHandlers::debugAcknowledgeEvent(hDebug, event); } -ze_result_t zetDebugGetRegisterSetProperties( +ze_result_t ZE_APICALL zetDebugGetRegisterSetProperties( zet_device_handle_t hDevice, uint32_t *pCount, zet_debug_regset_properties_t *pRegisterSetProperties) { return L0::DebugApiHandlers::debugGetRegisterSetProperties(hDevice, pCount, pRegisterSetProperties); } -ze_result_t zetDebugReadRegisters( +ze_result_t ZE_APICALL zetDebugReadRegisters( zet_debug_session_handle_t hDebug, ze_device_thread_t thread, uint32_t type, @@ -90,7 +90,7 @@ ze_result_t zetDebugReadRegisters( return L0::DebugApiHandlers::debugReadRegisters(hDebug, thread, type, start, count, pRegisterValues); } -ze_result_t zetDebugWriteRegisters( +ze_result_t ZE_APICALL zetDebugWriteRegisters( zet_debug_session_handle_t hDebug, ze_device_thread_t thread, uint32_t type, @@ -100,7 +100,7 @@ ze_result_t zetDebugWriteRegisters( return L0::DebugApiHandlers::debugWriteRegisters(hDebug, thread, type, start, count, pRegisterValues); } -ze_result_t zetDebugGetThreadRegisterSetProperties( +ze_result_t ZE_APICALL zetDebugGetThreadRegisterSetProperties( zet_debug_session_handle_t hDebug, ze_device_thread_t thread, uint32_t *pCount, diff --git a/level_zero/api/tools/zet_metric_api_entrypoints.h b/level_zero/api/tools/zet_metric_api_entrypoints.h index be4015d581..b50d9ba547 100644 --- a/level_zero/api/tools/zet_metric_api_entrypoints.h +++ b/level_zero/api/tools/zet_metric_api_entrypoints.h @@ -15,33 +15,33 @@ namespace L0 { -ze_result_t zetMetricGroupGet( +ze_result_t ZE_APICALL zetMetricGroupGet( zet_device_handle_t hDevice, uint32_t *pCount, zet_metric_group_handle_t *phMetricGroups) { return L0::metricGroupGet(hDevice, pCount, phMetricGroups); } -ze_result_t zetMetricGroupGetProperties( +ze_result_t ZE_APICALL zetMetricGroupGetProperties( zet_metric_group_handle_t hMetricGroup, zet_metric_group_properties_t *pProperties) { return L0::MetricGroup::fromHandle(hMetricGroup)->getProperties(pProperties); } -ze_result_t zetMetricGet( +ze_result_t ZE_APICALL zetMetricGet( zet_metric_group_handle_t hMetricGroup, uint32_t *pCount, zet_metric_handle_t *phMetrics) { return L0::MetricGroup::fromHandle(hMetricGroup)->metricGet(pCount, phMetrics); } -ze_result_t zetMetricGetProperties( +ze_result_t ZE_APICALL zetMetricGetProperties( zet_metric_handle_t hMetric, zet_metric_properties_t *pProperties) { return L0::Metric::fromHandle(hMetric)->getProperties(pProperties); } -ze_result_t zetMetricGroupCalculateMetricValues( +ze_result_t ZE_APICALL zetMetricGroupCalculateMetricValues( zet_metric_group_handle_t hMetricGroup, zet_metric_group_calculation_type_t type, size_t rawDataSize, @@ -51,7 +51,7 @@ ze_result_t zetMetricGroupCalculateMetricValues( return L0::MetricGroup::fromHandle(hMetricGroup)->calculateMetricValues(type, rawDataSize, pRawData, pMetricValueCount, pMetricValues); } -ze_result_t zetContextActivateMetricGroups( +ze_result_t ZE_APICALL zetContextActivateMetricGroups( zet_context_handle_t hContext, zet_device_handle_t hDevice, uint32_t count, @@ -59,7 +59,7 @@ ze_result_t zetContextActivateMetricGroups( return L0::Context::fromHandle(hContext)->activateMetricGroups(hDevice, count, phMetricGroups); } -ze_result_t zetMetricStreamerOpen( +ze_result_t ZE_APICALL zetMetricStreamerOpen( zet_context_handle_t hContext, zet_device_handle_t hDevice, zet_metric_group_handle_t hMetricGroup, @@ -69,19 +69,19 @@ ze_result_t zetMetricStreamerOpen( return L0::metricStreamerOpen(hContext, hDevice, hMetricGroup, pDesc, hNotificationEvent, phMetricStreamer); } -ze_result_t zetCommandListAppendMetricStreamerMarker( +ze_result_t ZE_APICALL zetCommandListAppendMetricStreamerMarker( ze_command_list_handle_t hCommandList, zet_metric_streamer_handle_t hMetricStreamer, uint32_t value) { return L0::CommandList::fromHandle(hCommandList)->appendMetricStreamerMarker(hMetricStreamer, value); } -ze_result_t zetMetricStreamerClose( +ze_result_t ZE_APICALL zetMetricStreamerClose( zet_metric_streamer_handle_t hMetricStreamer) { return L0::MetricStreamer::fromHandle(hMetricStreamer)->close(); } -ze_result_t zetMetricStreamerReadData( +ze_result_t ZE_APICALL zetMetricStreamerReadData( zet_metric_streamer_handle_t hMetricStreamer, uint32_t maxReportCount, size_t *pRawDataSize, @@ -89,7 +89,7 @@ ze_result_t zetMetricStreamerReadData( return L0::MetricStreamer::fromHandle(hMetricStreamer)->readData(maxReportCount, pRawDataSize, pRawData); } -ze_result_t zetMetricQueryPoolCreate( +ze_result_t ZE_APICALL zetMetricQueryPoolCreate( zet_context_handle_t hContext, zet_device_handle_t hDevice, zet_metric_group_handle_t hMetricGroup, @@ -98,35 +98,35 @@ ze_result_t zetMetricQueryPoolCreate( return L0::metricQueryPoolCreate(hContext, hDevice, hMetricGroup, desc, phMetricQueryPool); } -ze_result_t zetMetricQueryPoolDestroy( +ze_result_t ZE_APICALL zetMetricQueryPoolDestroy( zet_metric_query_pool_handle_t hMetricQueryPool) { return L0::MetricQueryPool::fromHandle(hMetricQueryPool)->destroy(); } -ze_result_t zetMetricQueryCreate( +ze_result_t ZE_APICALL zetMetricQueryCreate( zet_metric_query_pool_handle_t hMetricQueryPool, uint32_t index, zet_metric_query_handle_t *phMetricQuery) { return L0::MetricQueryPool::fromHandle(hMetricQueryPool)->metricQueryCreate(index, phMetricQuery); } -ze_result_t zetMetricQueryDestroy( +ze_result_t ZE_APICALL zetMetricQueryDestroy( zet_metric_query_handle_t hMetricQuery) { return L0::MetricQuery::fromHandle(hMetricQuery)->destroy(); } -ze_result_t zetMetricQueryReset( +ze_result_t ZE_APICALL zetMetricQueryReset( zet_metric_query_handle_t hMetricQuery) { return L0::MetricQuery::fromHandle(hMetricQuery)->reset(); } -ze_result_t zetCommandListAppendMetricQueryBegin( +ze_result_t ZE_APICALL zetCommandListAppendMetricQueryBegin( zet_command_list_handle_t hCommandList, zet_metric_query_handle_t hMetricQuery) { return L0::CommandList::fromHandle(hCommandList)->appendMetricQueryBegin(hMetricQuery); } -ze_result_t zetCommandListAppendMetricQueryEnd( +ze_result_t ZE_APICALL zetCommandListAppendMetricQueryEnd( zet_command_list_handle_t hCommandList, zet_metric_query_handle_t hMetricQuery, ze_event_handle_t hSignalEvent, @@ -135,12 +135,12 @@ ze_result_t zetCommandListAppendMetricQueryEnd( return L0::CommandList::fromHandle(hCommandList)->appendMetricQueryEnd(hMetricQuery, hSignalEvent, numWaitEvents, phWaitEvents); } -ze_result_t zetCommandListAppendMetricMemoryBarrier( +ze_result_t ZE_APICALL zetCommandListAppendMetricMemoryBarrier( zet_command_list_handle_t hCommandList) { return L0::CommandList::fromHandle(hCommandList)->appendMetricMemoryBarrier(); } -ze_result_t zetMetricQueryGetData( +ze_result_t ZE_APICALL zetMetricQueryGetData( zet_metric_query_handle_t hMetricQuery, size_t *pRawDataSize, uint8_t *pRawData) { diff --git a/level_zero/api/tools/zet_module_api_entrypoints.h b/level_zero/api/tools/zet_module_api_entrypoints.h index c333ee632c..81eddad651 100644 --- a/level_zero/api/tools/zet_module_api_entrypoints.h +++ b/level_zero/api/tools/zet_module_api_entrypoints.h @@ -1,5 +1,5 @@ /* - * Copyright (C) 2020-2022 Intel Corporation + * Copyright (C) 2020-2025 Intel Corporation * * SPDX-License-Identifier: MIT * @@ -12,7 +12,7 @@ #include namespace L0 { -ze_result_t zetModuleGetDebugInfo( +ze_result_t ZE_APICALL zetModuleGetDebugInfo( zet_module_handle_t hModule, zet_module_debug_info_format_t format, size_t *pSize, @@ -20,7 +20,7 @@ ze_result_t zetModuleGetDebugInfo( return L0::Module::fromHandle(hModule)->getDebugInfo(pSize, pDebugInfo); } -ze_result_t zetKernelGetProfileInfo( +ze_result_t ZE_APICALL zetKernelGetProfileInfo( zet_kernel_handle_t hKernel, zet_profile_properties_t *pProfileProperties) { return L0::Kernel::fromHandle(hKernel)->getProfileInfo(pProfileProperties);