From aecc19d12a731fa178cc187df225bb59a72a5ae4 Mon Sep 17 00:00:00 2001 From: "Neil R. Spruit" Date: Fri, 23 May 2025 12:23:28 -0700 Subject: [PATCH] Rename the static build define from DYNAMIC_LOAD_LOADER to L0_STATIC_LOADER_BUILD Signed-off-by: Neil R. Spruit --- scripts/templates/libapi.cpp.mako | 8 +- scripts/templates/libddi.cpp.mako | 4 +- source/CMakeLists.txt | 2 +- source/lib/linux/lib_init.cpp | 2 +- source/lib/windows/lib_init.cpp | 4 +- source/lib/ze_lib.cpp | 30 +- source/lib/ze_lib.h | 6 +- source/lib/ze_libapi.cpp | 406 +++++++++++++------------- source/lib/ze_libddi.cpp | 4 +- source/lib/zel_tracing_libddi.cpp | 2 +- source/lib/zes_libapi.cpp | 298 +++++++++---------- source/lib/zes_libddi.cpp | 4 +- source/lib/zet_libapi.cpp | 138 ++++----- source/lib/zet_libddi.cpp | 4 +- source/loader/linux/loader_init.cpp | 2 +- source/loader/windows/loader_init.cpp | 2 +- 16 files changed, 458 insertions(+), 458 deletions(-) diff --git a/scripts/templates/libapi.cpp.mako b/scripts/templates/libapi.cpp.mako index b19e69fb..c36c9618 100644 --- a/scripts/templates/libapi.cpp.mako +++ b/scripts/templates/libapi.cpp.mako @@ -56,7 +56,7 @@ ${th.make_func_name(n, tags, obj)}( { %if re.match("Init", obj['name']): %if re.match("zes", n): - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD if (!${x}_lib::context) { ${x}_lib::context = new ${x}_lib::context_t; } @@ -87,7 +87,7 @@ ${th.make_func_name(n, tags, obj)}( %else: %if re.match("InitDrivers", obj['name']): ${x}_result_t result = ${X}_RESULT_SUCCESS; - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD if (!${x}_lib::context) { ${x}_lib::context = new ${x}_lib::context_t; } @@ -124,7 +124,7 @@ ${th.make_func_name(n, tags, obj)}( return result; %else: static ${x}_result_t result = ${X}_RESULT_SUCCESS; - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD if (!${x}_lib::context) { ${x}_lib::context = new ${x}_lib::context_t; } @@ -160,7 +160,7 @@ ${th.make_func_name(n, tags, obj)}( } %endif %else: - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ${X}_RESULT_SUCCESS; if(ze_lib::destruction) { return ${X}_RESULT_ERROR_UNINITIALIZED; diff --git a/scripts/templates/libddi.cpp.mako b/scripts/templates/libddi.cpp.mako index a965c5e4..a4229f80 100644 --- a/scripts/templates/libddi.cpp.mako +++ b/scripts/templates/libddi.cpp.mako @@ -17,7 +17,7 @@ from templates import helper as th * */ #include "${x}_lib.h" -#ifndef DYNAMIC_LOAD_LOADER +#ifndef L0_STATIC_LOADER_BUILD #include "${n}_ddi.h" #endif @@ -25,7 +25,7 @@ namespace ${x}_lib { /////////////////////////////////////////////////////////////////////////////// -#ifdef DYNAMIC_LOAD_LOADER +#ifdef L0_STATIC_LOADER_BUILD __zedlllocal ${x}_result_t context_t::${n}DdiTableInit(ze_api_version_t version) { ${x}_result_t result = ${X}_RESULT_SUCCESS; diff --git a/source/CMakeLists.txt b/source/CMakeLists.txt index 0ca11962..2ec4b8db 100644 --- a/source/CMakeLists.txt +++ b/source/CMakeLists.txt @@ -19,7 +19,7 @@ if (BUILD_STATIC) "" ${CMAKE_CURRENT_BINARY_DIR}/ZeLoaderVersion.rc ) - add_definitions(-DDYNAMIC_LOAD_LOADER="1") + add_definitions(-DL0_STATIC_LOADER_BUILD="1") else() message(STATUS "Building loader as dynamic library") add_library(${TARGET_LOADER_NAME} diff --git a/source/lib/linux/lib_init.cpp b/source/lib/linux/lib_init.cpp index 399736c7..97e4bde2 100644 --- a/source/lib/linux/lib_init.cpp +++ b/source/lib/linux/lib_init.cpp @@ -10,7 +10,7 @@ namespace ze_lib { -#ifndef DYNAMIC_LOAD_LOADER +#ifndef L0_STATIC_LOADER_BUILD void __attribute__((constructor)) createLibContext() { context = new context_t; } diff --git a/source/lib/windows/lib_init.cpp b/source/lib/windows/lib_init.cpp index db47b9a9..b76bace6 100644 --- a/source/lib/windows/lib_init.cpp +++ b/source/lib/windows/lib_init.cpp @@ -7,13 +7,13 @@ */ #include "../ze_lib.h" -#ifndef DYNAMIC_LOAD_LOADER +#ifndef L0_STATIC_LOADER_BUILD #include "../loader/ze_loader_internal.h" #endif namespace ze_lib { -#ifndef DYNAMIC_LOAD_LOADER +#ifndef L0_STATIC_LOADER_BUILD extern "C" BOOL APIENTRY DllMain(HINSTANCE hinstDLL, DWORD fdwReason, LPVOID lpvReserved) { if (fdwReason == DLL_PROCESS_DETACH) { delete context; diff --git a/source/lib/ze_lib.cpp b/source/lib/ze_lib.cpp index b4554d52..f82080f0 100644 --- a/source/lib/ze_lib.cpp +++ b/source/lib/ze_lib.cpp @@ -18,7 +18,7 @@ namespace ze_lib { /////////////////////////////////////////////////////////////////////////////// context_t *context = nullptr; - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD void context_at_exit_destructor() { if (ze_lib::context) { @@ -69,7 +69,7 @@ namespace ze_lib /////////////////////////////////////////////////////////////////////////////// __zedlllocal context_t::~context_t() { -#ifdef DYNAMIC_LOAD_LOADER +#ifdef L0_STATIC_LOADER_BUILD if (loaderTeardownRegistrationEnabled && !loaderTeardownCallbackReceived) { loaderTeardownCallback(loaderTeardownCallbackIndex); } @@ -92,7 +92,7 @@ namespace ze_lib { ze_result_t result; ze_api_version_t version = ZE_API_VERSION_CURRENT; -#ifdef DYNAMIC_LOAD_LOADER +#ifdef L0_STATIC_LOADER_BUILD std::string loaderLibraryPath; auto loaderLibraryPathEnv = getenv_string("ZEL_LIBRARY_PATH"); if (!loaderLibraryPathEnv.empty()) { @@ -213,7 +213,7 @@ namespace ze_lib // Given zesInit, then zesDrivers needs to be used as the sysmanInstanceDrivers; bool loaderContextAccessAllowed = true; -#ifdef DYNAMIC_LOAD_LOADER +#ifdef L0_STATIC_LOADER_BUILD loaderContextAccessAllowed = false; loader::context_t *loaderContext = nullptr; #else @@ -264,7 +264,7 @@ namespace ze_lib // Init the stored ddi tables for the tracing layer if( ZE_RESULT_SUCCESS == result ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD if (loaderTracingLayerInit) { result = loaderTracingLayerInit(this->pTracingZeDdiTable); } @@ -280,7 +280,7 @@ namespace ze_lib // Check which drivers support the ze_driver_flag_t specified // No need to check if only initializing sysman bool requireDdiReinit = false; - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD if (zeInitDriversSupport) { typedef ze_result_t (ZE_APICALL *zelLoaderDriverCheck_t)(ze_init_flags_t flags, ze_init_driver_type_desc_t* desc, ze_global_dditable_t *globalInitStored, zes_global_dditable_t *sysmanGlobalInitStored, bool *requireDdiReinit, bool sysmanOnly); auto loaderDriverCheck = reinterpret_cast( @@ -341,7 +341,7 @@ namespace ze_lib if( ZE_RESULT_SUCCESS == result ) { -#ifdef DYNAMIC_LOAD_LOADER +#ifdef L0_STATIC_LOADER_BUILD // Init Dynamic Loader's Lib Context: auto initDriversLoader = reinterpret_cast( GET_FUNCTION_PTR(loader, "zeInitDrivers") ); @@ -378,7 +378,7 @@ namespace ze_lib #endif isInitialized = true; } - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD std::call_once(ze_lib::context->initTeardownCallbacksOnce, [this]() { if (!delayContextDestruction) { std::atexit(context_at_exit_destructor); @@ -416,7 +416,7 @@ zelLoaderGetVersions( size_t *num_elems, //Pointer to num versions to get. zel_component_version_t *versions) //Pointer to array of versions. If set to NULL, num_elems is returned { -#ifdef DYNAMIC_LOAD_LOADER +#ifdef L0_STATIC_LOADER_BUILD if(nullptr == ze_lib::context->loader) return ZE_RESULT_ERROR_UNINITIALIZED; typedef ze_result_t (ZE_APICALL *zelLoaderGetVersions_t)(size_t *num_elems, zel_component_version_t *versions); @@ -436,7 +436,7 @@ zelLoaderTranslateHandle( void **handleOut) { -#ifdef DYNAMIC_LOAD_LOADER +#ifdef L0_STATIC_LOADER_BUILD if(nullptr == ze_lib::context->loader) return ZE_RESULT_ERROR_UNINITIALIZED; typedef ze_result_t (ZE_APICALL *zelLoaderTranslateHandleInternal_t)(zel_handle_type_t handleType, void *handleIn, void **handleOut); @@ -470,7 +470,7 @@ zelSetDriverTeardown() void ZE_APICALL zelSetDelayLoaderContextTeardown() { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD if (!ze_lib::delayContextDestruction) { ze_lib::delayContextDestruction = true; } @@ -539,7 +539,7 @@ zelCheckIsLoaderInTearDown() { if (ze_lib::destruction || ze_lib::context == nullptr) { return true; } - #if defined(DYNAMIC_LOAD_LOADER) && defined(_WIN32) + #if defined(L0_STATIC_LOADER_BUILD) && defined(_WIN32) static bool loaderIsStable = true; if (!loaderIsStable) { if (ze_lib::context->debugTraceEnabled) { @@ -594,7 +594,7 @@ zelCheckIsLoaderInTearDown() { void ZE_APICALL zelLoaderContextTeardown() { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD if (ze_lib::delayContextDestruction && ze_lib::context) { delete ze_lib::context; ze_lib::context = nullptr; @@ -605,7 +605,7 @@ zelLoaderContextTeardown() ze_result_t ZE_APICALL zelEnableTracingLayer() { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD if(nullptr == ze_lib::context->loader) return ZE_RESULT_ERROR_UNINITIALIZED; typedef ze_result_t (ZE_APICALL *zelEnableTracingLayerInternal_t)(); @@ -626,7 +626,7 @@ zelEnableTracingLayer() ze_result_t ZE_APICALL zelDisableTracingLayer() { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD if(nullptr == ze_lib::context->loader) return ZE_RESULT_ERROR_UNINITIALIZED; typedef ze_result_t (ZE_APICALL *zelDisableTracingLayerInternal_t)(); diff --git a/source/lib/ze_lib.h b/source/lib/ze_lib.h index 4e829f1f..44d85bfc 100644 --- a/source/lib/ze_lib.h +++ b/source/lib/ze_lib.h @@ -31,7 +31,7 @@ namespace ze_lib class __zedlllocal context_t { public: -#ifdef DYNAMIC_LOAD_LOADER +#ifdef L0_STATIC_LOADER_BUILD HMODULE loader = nullptr; #endif @@ -179,7 +179,7 @@ namespace ze_lib std::atomic teardownCallbacksCount{0}; std::map teardownCallbacks; std::mutex teardownCallbacksMutex; - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD std::once_flag initTeardownCallbacksOnce; zel_application_teardown_callback_t loaderTeardownCallback = nullptr; uint32_t loaderTeardownCallbackIndex = 0; @@ -188,7 +188,7 @@ namespace ze_lib extern bool destruction; extern context_t *context; - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD extern bool delayContextDestruction; extern bool loaderTeardownCallbackReceived; extern bool loaderTeardownRegistrationEnabled; diff --git a/source/lib/ze_libapi.cpp b/source/lib/ze_libapi.cpp index d6a2f55f..a18b5064 100644 --- a/source/lib/ze_libapi.cpp +++ b/source/lib/ze_libapi.cpp @@ -46,7 +46,7 @@ zeInit( ) { static ze_result_t result = ZE_RESULT_SUCCESS; - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD if (!ze_lib::context) { ze_lib::context = new ze_lib::context_t; } @@ -120,7 +120,7 @@ zeDriverGet( ///< shall only retrieve that number of drivers. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -223,7 +223,7 @@ zeInitDrivers( ) { ze_result_t result = ZE_RESULT_SUCCESS; - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD if (!ze_lib::context) { ze_lib::context = new ze_lib::context_t; } @@ -283,7 +283,7 @@ zeDriverGetApiVersion( ze_api_version_t* version ///< [out] api version ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -343,7 +343,7 @@ zeDriverGetProperties( ze_driver_properties_t* pDriverProperties ///< [in,out] query result for driver properties ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -399,7 +399,7 @@ zeDriverGetIpcProperties( ze_driver_ipc_properties_t* pIpcProperties ///< [in,out] query result for IPC properties ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -468,7 +468,7 @@ zeDriverGetExtensionProperties( ///< then driver shall only retrieve that number of extension properties. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -527,7 +527,7 @@ zeDriverGetExtensionFunctionAddress( void** ppFunctionAddress ///< [out] pointer to function pointer ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -590,7 +590,7 @@ zeDriverGetLastErrorDescription( ///< cause of error. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -658,7 +658,7 @@ zeDeviceGet( ///< shall only retrieve that number of devices. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -722,7 +722,7 @@ zeDeviceGetRootDevice( ze_device_handle_t* phRootDevice ///< [in,out] parent root device. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -795,7 +795,7 @@ zeDeviceGetSubDevices( ///< shall only retrieve that number of sub-devices. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -855,7 +855,7 @@ zeDeviceGetProperties( ze_device_properties_t* pDeviceProperties ///< [in,out] query result for device properties ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -915,7 +915,7 @@ zeDeviceGetComputeProperties( ze_device_compute_properties_t* pComputeProperties ///< [in,out] query result for compute properties ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -971,7 +971,7 @@ zeDeviceGetModuleProperties( ze_device_module_properties_t* pModuleProperties///< [in,out] query result for module properties ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1047,7 +1047,7 @@ zeDeviceGetCommandQueueGroupProperties( ///< queue group properties. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1122,7 +1122,7 @@ zeDeviceGetMemoryProperties( ///< driver shall only retrieve that number of memory properties. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1182,7 +1182,7 @@ zeDeviceGetMemoryAccessProperties( ze_device_memory_access_properties_t* pMemAccessProperties ///< [in,out] query result for memory access properties ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1250,7 +1250,7 @@ zeDeviceGetCacheProperties( ///< driver shall only retrieve that number of cache properties. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1307,7 +1307,7 @@ zeDeviceGetImageProperties( ze_device_image_properties_t* pImageProperties ///< [in,out] query result for image properties ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1363,7 +1363,7 @@ zeDeviceGetExternalMemoryProperties( ze_device_external_memory_properties_t* pExternalMemoryProperties ///< [in,out] query result for external memory properties ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1422,7 +1422,7 @@ zeDeviceGetP2PProperties( ze_device_p2p_properties_t* pP2PProperties ///< [in,out] Peer-to-Peer properties between source and peer device ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1494,7 +1494,7 @@ zeDeviceCanAccessPeer( ze_bool_t* value ///< [out] returned access capability ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1554,7 +1554,7 @@ zeDeviceGetStatus( ze_device_handle_t hDevice ///< [in] handle of the device ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1617,7 +1617,7 @@ zeDeviceGetGlobalTimestamps( ///< Host's global timestamp value. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1679,7 +1679,7 @@ zeContextCreate( ze_context_handle_t* phContext ///< [out] pointer to handle of context object created ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1753,7 +1753,7 @@ zeContextCreateEx( ze_context_handle_t* phContext ///< [out] pointer to handle of context object created ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1812,7 +1812,7 @@ zeContextDestroy( ze_context_handle_t hContext ///< [in][release] handle of context object to destroy ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1870,7 +1870,7 @@ zeContextGetStatus( ze_context_handle_t hContext ///< [in] handle of context object ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1942,7 +1942,7 @@ zeCommandQueueCreate( ze_command_queue_handle_t* phCommandQueue ///< [out] pointer to handle of command queue object created ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2007,7 +2007,7 @@ zeCommandQueueDestroy( ze_command_queue_handle_t hCommandQueue ///< [in][release] handle of command queue object to destroy ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2089,7 +2089,7 @@ zeCommandQueueExecuteCommandLists( ze_fence_handle_t hFence ///< [in][optional] handle of the fence to signal on completion ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2151,7 +2151,7 @@ zeCommandQueueSynchronize( ///< value allowed by the accuracy of those dependencies. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2207,7 +2207,7 @@ zeCommandQueueGetOrdinal( uint32_t* pOrdinal ///< [out] command queue group ordinal ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2263,7 +2263,7 @@ zeCommandQueueGetIndex( uint32_t* pIndex ///< [out] command queue index within the group ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2330,7 +2330,7 @@ zeCommandListCreate( ze_command_list_handle_t* phCommandList ///< [out] pointer to handle of command list object created ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2405,7 +2405,7 @@ zeCommandListCreateImmediate( ze_command_list_handle_t* phCommandList ///< [out] pointer to handle of command list object created ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2464,7 +2464,7 @@ zeCommandListDestroy( ze_command_list_handle_t hCommandList ///< [in][release] handle of command list object to destroy ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2518,7 +2518,7 @@ zeCommandListClose( ze_command_list_handle_t hCommandList ///< [in] handle of command list object to close ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2575,7 +2575,7 @@ zeCommandListReset( ze_command_list_handle_t hCommandList ///< [in] handle of command list object to reset ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2652,7 +2652,7 @@ zeCommandListAppendWriteGlobalTimestamp( ///< on before executing query ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2723,7 +2723,7 @@ zeCommandListHostSynchronize( ///< value allowed by the accuracy of those dependencies. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2779,7 +2779,7 @@ zeCommandListGetDeviceHandle( ze_device_handle_t* phDevice ///< [out] handle of the device on which the command list was created ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2835,7 +2835,7 @@ zeCommandListGetContextHandle( ze_context_handle_t* phContext ///< [out] handle of the context on which the command list was created ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2892,7 +2892,7 @@ zeCommandListGetOrdinal( uint32_t* pOrdinal ///< [out] command queue group ordinal to which command list is submitted ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2954,7 +2954,7 @@ zeCommandListImmediateGetIndex( ///< command list is submitted ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3011,7 +3011,7 @@ zeCommandListIsImmediate( ///< command list (true) or not (false) ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3087,7 +3087,7 @@ zeCommandListAppendBarrier( ///< on before executing barrier ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3163,7 +3163,7 @@ zeCommandListAppendMemoryRangesBarrier( ///< on before executing barrier ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3224,7 +3224,7 @@ zeContextSystemBarrier( ze_device_handle_t hDevice ///< [in] handle of the device ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3308,7 +3308,7 @@ zeCommandListAppendMemoryCopy( ///< on before launching ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3396,7 +3396,7 @@ zeCommandListAppendMemoryFill( ///< on before launching ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3489,7 +3489,7 @@ zeCommandListAppendMemoryCopyRegion( ///< on before launching ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3569,7 +3569,7 @@ zeCommandListAppendMemoryCopyFromContext( ///< on before launching ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3645,7 +3645,7 @@ zeCommandListAppendImageCopy( ///< on before launching ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3723,7 +3723,7 @@ zeCommandListAppendImageCopyRegion( ///< on before launching ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3806,7 +3806,7 @@ zeCommandListAppendImageCopyToMemory( ///< on before launching ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3889,7 +3889,7 @@ zeCommandListAppendImageCopyFromMemory( ///< on before launching ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3968,7 +3968,7 @@ zeCommandListAppendMemoryPrefetch( size_t size ///< [in] size in bytes of the memory range to prefetch ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4047,7 +4047,7 @@ zeCommandListAppendMemAdvise( ze_memory_advice_t advice ///< [in] Memory advice for the memory range ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4118,7 +4118,7 @@ zeEventPoolCreate( ze_event_pool_handle_t* phEventPool ///< [out] pointer handle of event pool object created ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4179,7 +4179,7 @@ zeEventPoolDestroy( ze_event_pool_handle_t hEventPool ///< [in][release] handle of event pool object to destroy ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4250,7 +4250,7 @@ zeEventCreate( ze_event_handle_t* phEvent ///< [out] pointer to handle of event object created ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4314,7 +4314,7 @@ zeEventDestroy( ze_event_handle_t hEvent ///< [in][release] handle of event object to destroy ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4372,7 +4372,7 @@ zeEventPoolGetIpcHandle( ze_ipc_event_pool_handle_t* phIpc ///< [out] Returned IPC event handle ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4436,7 +4436,7 @@ zeEventPoolPutIpcHandle( ze_ipc_event_pool_handle_t hIpc ///< [in] IPC event pool handle ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4510,7 +4510,7 @@ zeEventPoolOpenIpcHandle( ze_event_pool_handle_t* phEventPool ///< [out] pointer handle of event pool object created ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4565,7 +4565,7 @@ zeEventPoolCloseIpcHandle( ze_event_pool_handle_t hEventPool ///< [in][release] handle of event pool object ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4636,7 +4636,7 @@ zeCommandListAppendSignalEvent( ze_event_handle_t hEvent ///< [in] handle of the event ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4700,7 +4700,7 @@ zeCommandListAppendWaitOnEvents( ///< continuing ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4763,7 +4763,7 @@ zeEventHostSignal( ze_event_handle_t hEvent ///< [in] handle of the event ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4830,7 +4830,7 @@ zeEventHostSynchronize( ///< value allowed by the accuracy of those dependencies. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4891,7 +4891,7 @@ zeEventQueryStatus( ze_event_handle_t hEvent ///< [in] handle of the event ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4957,7 +4957,7 @@ zeCommandListAppendEventReset( ze_event_handle_t hEvent ///< [in] handle of the event ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5015,7 +5015,7 @@ zeEventHostReset( ze_event_handle_t hEvent ///< [in] handle of the event ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5079,7 +5079,7 @@ zeEventQueryKernelTimestamp( ze_kernel_timestamp_result_t* dstptr ///< [in,out] pointer to memory for where timestamp result will be written. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5164,7 +5164,7 @@ zeCommandListAppendQueryKernelTimestamps( ///< on before executing query ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5220,7 +5220,7 @@ zeEventGetEventPool( ze_event_pool_handle_t* phEventPool ///< [out] handle of the event pool for the event ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5278,7 +5278,7 @@ zeEventGetSignalScope( ///< triggered. May be 0 or a valid combination of ::ze_event_scope_flag_t. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5336,7 +5336,7 @@ zeEventGetWaitScope( ///< May be 0 or a valid combination of ::ze_event_scope_flag_t. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5392,7 +5392,7 @@ zeEventPoolGetContextHandle( ze_context_handle_t* phContext ///< [out] handle of the context on which the event pool was created ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5449,7 +5449,7 @@ zeEventPoolGetFlags( ///< valid combination of ::ze_event_pool_flag_t ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5517,7 +5517,7 @@ zeFenceCreate( ze_fence_handle_t* phFence ///< [out] pointer to handle of fence object created ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5580,7 +5580,7 @@ zeFenceDestroy( ze_fence_handle_t hFence ///< [in][release] handle of fence object to destroy ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5647,7 +5647,7 @@ zeFenceHostSynchronize( ///< value allowed by the accuracy of those dependencies. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5707,7 +5707,7 @@ zeFenceQueryStatus( ze_fence_handle_t hFence ///< [in] handle of the fence ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5764,7 +5764,7 @@ zeFenceReset( ze_fence_handle_t hFence ///< [in] handle of the fence ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5825,7 +5825,7 @@ zeImageGetProperties( ze_image_properties_t* pImageProperties ///< [out] pointer to image properties ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5895,7 +5895,7 @@ zeImageCreate( ze_image_handle_t* phImage ///< [out] pointer to handle of image object created ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5954,7 +5954,7 @@ zeImageDestroy( ze_image_handle_t hImage ///< [in][release] handle of image object to destroy ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -6042,7 +6042,7 @@ zeMemAllocShared( void** pptr ///< [out] pointer to shared allocation ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -6118,7 +6118,7 @@ zeMemAllocDevice( void** pptr ///< [out] pointer to device allocation ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -6194,7 +6194,7 @@ zeMemAllocHost( void** pptr ///< [out] pointer to host allocation ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -6259,7 +6259,7 @@ zeMemFree( void* ptr ///< [in][release] pointer to memory to free ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -6322,7 +6322,7 @@ zeMemGetAllocProperties( ze_device_handle_t* phDevice ///< [out][optional] device associated with this allocation ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -6379,7 +6379,7 @@ zeMemGetAddressRange( size_t* pSize ///< [in,out][optional] size of the allocation ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -6442,7 +6442,7 @@ zeMemGetIpcHandle( ze_ipc_mem_handle_t* pIpcHandle ///< [out] Returned IPC memory handle ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -6503,7 +6503,7 @@ zeMemGetIpcHandleFromFileDescriptorExp( ze_ipc_mem_handle_t* pIpcHandle ///< [out] Returned IPC memory handle ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -6562,7 +6562,7 @@ zeMemGetFileDescriptorFromIpcHandleExp( uint64_t* pHandle ///< [out] Returned file descriptor ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -6625,7 +6625,7 @@ zeMemPutIpcHandle( ze_ipc_mem_handle_t handle ///< [in] IPC memory handle ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -6695,7 +6695,7 @@ zeMemOpenIpcHandle( void** pptr ///< [out] pointer to device allocation in this process ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -6754,7 +6754,7 @@ zeMemCloseIpcHandle( const void* ptr ///< [in][release] pointer to device allocation in this process ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -6833,7 +6833,7 @@ zeMemSetAtomicAccessAttributeExp( ///< Must be 0 (default) or a valid combination of ::ze_memory_atomic_attr_exp_flag_t. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -6896,7 +6896,7 @@ zeMemGetAtomicAccessAttributeExp( ze_memory_atomic_attr_exp_flags_t* pAttr ///< [out] Atomic access attributes for the specified range ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -6973,7 +6973,7 @@ zeModuleCreate( ze_module_build_log_handle_t* phBuildLog ///< [out][optional] pointer to handle of module's build log. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7034,7 +7034,7 @@ zeModuleDestroy( ze_module_handle_t hModule ///< [in][release] handle of the module ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7117,7 +7117,7 @@ zeModuleDynamicLink( ze_module_build_log_handle_t* phLinkLog ///< [out][optional] pointer to handle of dynamic link log. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7176,7 +7176,7 @@ zeModuleBuildLogDestroy( ze_module_build_log_handle_t hModuleBuildLog ///< [in][release] handle of the module build log object. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7235,7 +7235,7 @@ zeModuleBuildLogGetString( char* pBuildLog ///< [in,out][optional] pointer to null-terminated string of the log. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7300,7 +7300,7 @@ zeModuleGetNativeBinary( uint8_t* pModuleNativeBinary ///< [in,out][optional] byte pointer to native binary ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7363,7 +7363,7 @@ zeModuleGetGlobalPointer( void** pptr ///< [in,out][optional] device visible pointer ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7426,7 +7426,7 @@ zeModuleGetKernelNames( ///< only retrieve that number of names. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7482,7 +7482,7 @@ zeModuleGetProperties( ze_module_properties_t* pModuleProperties ///< [in,out] query result for module properties. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7547,7 +7547,7 @@ zeKernelCreate( ze_kernel_handle_t* phKernel ///< [out] handle of the Function object ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7606,7 +7606,7 @@ zeKernelDestroy( ze_kernel_handle_t hKernel ///< [in][release] handle of the kernel object ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7670,7 +7670,7 @@ zeModuleGetFunctionPointer( void** pfnFunction ///< [out] pointer to function. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7730,7 +7730,7 @@ zeKernelSetGroupSize( uint32_t groupSizeZ ///< [in] group size for Z dimension to use for this kernel ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7797,7 +7797,7 @@ zeKernelSuggestGroupSize( uint32_t* groupSizeZ ///< [out] recommended size of group for Z dimension ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7853,7 +7853,7 @@ zeKernelSuggestMaxCooperativeGroupCount( uint32_t* totalGroupCount ///< [out] recommended total group count. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7915,7 +7915,7 @@ zeKernelSetArgumentValue( ///< null then argument value is considered null. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7975,7 +7975,7 @@ zeKernelSetIndirectAccess( ze_kernel_indirect_access_flags_t flags ///< [in] kernel indirect access flags ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -8032,7 +8032,7 @@ zeKernelGetIndirectAccess( ze_kernel_indirect_access_flags_t* pFlags ///< [out] query result for kernel indirect access flags. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -8102,7 +8102,7 @@ zeKernelGetSourceAttributes( ///< create your own char *pString and then pass to this API with &pString. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -8163,7 +8163,7 @@ zeKernelSetCacheConfig( ///< must be 0 (default configuration) or a valid combination of ::ze_cache_config_flag_t. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -8219,7 +8219,7 @@ zeKernelGetProperties( ze_kernel_properties_t* pKernelProperties ///< [in,out] query result for kernel properties. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -8280,7 +8280,7 @@ zeKernelGetName( char* pName ///< [in,out][optional] char pointer to kernel name. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -8353,7 +8353,7 @@ zeCommandListAppendLaunchKernel( ///< on before launching ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -8430,7 +8430,7 @@ zeCommandListAppendLaunchCooperativeKernel( ///< on before launching ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -8509,7 +8509,7 @@ zeCommandListAppendLaunchKernelIndirect( ///< on before launching ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -8595,7 +8595,7 @@ zeCommandListAppendLaunchMultipleKernelsIndirect( ///< on before launching ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -8658,7 +8658,7 @@ zeContextMakeMemoryResident( size_t size ///< [in] size in bytes to make resident ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -8721,7 +8721,7 @@ zeContextEvictMemory( size_t size ///< [in] size in bytes to evict ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -8780,7 +8780,7 @@ zeContextMakeImageResident( ze_image_handle_t hImage ///< [in] handle of image to make resident ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -8841,7 +8841,7 @@ zeContextEvictImage( ze_image_handle_t hImage ///< [in] handle of image to make evict ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -8906,7 +8906,7 @@ zeSamplerCreate( ze_sampler_handle_t* phSampler ///< [out] handle of the sampler ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -8965,7 +8965,7 @@ zeSamplerDestroy( ze_sampler_handle_t hSampler ///< [in][release] handle of the sampler ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -9035,7 +9035,7 @@ zeVirtualMemReserve( void** pptr ///< [out] pointer to virtual reservation. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -9098,7 +9098,7 @@ zeVirtualMemFree( size_t size ///< [in] size in bytes to free; must be page aligned. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -9161,7 +9161,7 @@ zeVirtualMemQueryPageSize( ///< alignments. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -9232,7 +9232,7 @@ zePhysicalMemCreate( ze_physical_mem_handle_t* phPhysicalMemory ///< [out] pointer to handle of physical memory object created ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -9291,7 +9291,7 @@ zePhysicalMemDestroy( ze_physical_mem_handle_t hPhysicalMemory ///< [in][release] handle of physical memory object to destroy ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -9369,7 +9369,7 @@ zeVirtualMemMap( ///< range. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -9434,7 +9434,7 @@ zeVirtualMemUnmap( size_t size ///< [in] size in bytes to unmap; must be page aligned. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -9501,7 +9501,7 @@ zeVirtualMemSetAccessAttribute( ///< range. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -9571,7 +9571,7 @@ zeVirtualMemGetAccessAttribute( ///< that shares same access attribute. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -9630,7 +9630,7 @@ zeKernelSetGlobalOffsetExp( uint32_t offsetZ ///< [in] global offset for Z dimension to use for this kernel ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -9691,7 +9691,7 @@ zeKernelGetBinaryExp( uint8_t* pKernelBinary ///< [in,out] pointer to storage area for GEN ISA binary function. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -9753,7 +9753,7 @@ zeDeviceImportExternalSemaphoreExt( ze_external_semaphore_ext_handle_t* phSemaphore ///< [out] The handle of the external semaphore imported. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -9810,7 +9810,7 @@ zeDeviceReleaseExternalSemaphoreExt( ze_external_semaphore_ext_handle_t hSemaphore ///< [in] The handle of the external semaphore. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -9885,7 +9885,7 @@ zeCommandListAppendSignalExternalSemaphoreExt( ///< on before launching ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -9960,7 +9960,7 @@ zeCommandListAppendWaitExternalSemaphoreExt( ///< on before launching ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -10021,7 +10021,7 @@ zeRTASBuilderCreateExt( ze_rtas_builder_ext_handle_t* phBuilder ///< [out] handle of builder object ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -10083,7 +10083,7 @@ zeRTASBuilderGetBuildPropertiesExt( ze_rtas_builder_ext_properties_t* pProperties ///< [in,out] query result for builder properties ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -10145,7 +10145,7 @@ zeDriverRTASFormatCompatibilityCheckExt( ze_rtas_format_ext_t rtasFormatB ///< [in] operand B ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -10267,7 +10267,7 @@ zeRTASBuilderBuildExt( ///< bytes ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -10351,7 +10351,7 @@ zeRTASBuilderCommandListAppendCopyExt( ///< on before launching ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -10408,7 +10408,7 @@ zeRTASBuilderDestroyExt( ze_rtas_builder_ext_handle_t hBuilder ///< [in][release] handle of builder object to destroy ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -10466,7 +10466,7 @@ zeRTASParallelOperationCreateExt( ze_rtas_parallel_operation_ext_handle_t* phParallelOperation///< [out] handle of parallel operation object ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -10528,7 +10528,7 @@ zeRTASParallelOperationGetPropertiesExt( ze_rtas_parallel_operation_ext_properties_t* pProperties///< [in,out] query result for parallel operation properties ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -10581,7 +10581,7 @@ zeRTASParallelOperationJoinExt( ze_rtas_parallel_operation_ext_handle_t hParallelOperation ///< [in] handle of parallel operation object ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -10639,7 +10639,7 @@ zeRTASParallelOperationDestroyExt( ze_rtas_parallel_operation_ext_handle_t hParallelOperation ///< [in][release] handle of parallel operation object to destroy ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -10711,7 +10711,7 @@ zeDeviceGetVectorWidthPropertiesExt( ///< driver will return only the number requested. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -10773,7 +10773,7 @@ zeDeviceReserveCacheExt( ///< shall remove prior reservation ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -10833,7 +10833,7 @@ zeDeviceSetCacheAdviceExt( ze_cache_ext_region_t cacheRegion ///< [in] reservation region ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -10910,7 +10910,7 @@ zeEventQueryTimestampsExp( ///< shall only retrieve that number of timestamps. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -10972,7 +10972,7 @@ zeImageGetMemoryPropertiesExp( ze_image_memory_properties_exp_t* pMemoryProperties ///< [in,out] query result for image memory properties. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -11051,7 +11051,7 @@ zeImageViewCreateExt( ze_image_handle_t* phImageView ///< [out] pointer to handle of image object created for view ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -11133,7 +11133,7 @@ zeImageViewCreateExp( ze_image_handle_t* phImageView ///< [out] pointer to handle of image object created for view ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -11198,7 +11198,7 @@ zeKernelSchedulingHintExp( ze_scheduling_hint_exp_desc_t* pHint ///< [in] pointer to kernel scheduling hint descriptor ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -11258,7 +11258,7 @@ zeDevicePciGetPropertiesExt( ze_pci_ext_properties_t* pPciProperties ///< [in,out] returns the PCI properties of the device. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -11355,7 +11355,7 @@ zeCommandListAppendImageCopyToMemoryExt( ///< on before launching ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -11452,7 +11452,7 @@ zeCommandListAppendImageCopyFromMemoryExt( ///< on before launching ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -11509,7 +11509,7 @@ zeImageGetAllocPropertiesExt( ze_image_allocation_ext_properties_t* pImageAllocProperties ///< [in,out] query result for image allocation properties ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -11575,7 +11575,7 @@ zeModuleInspectLinkageExt( ///< contain separate lists of imports, un-resolvable imports, and exports. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -11640,7 +11640,7 @@ zeMemFreeExt( void* ptr ///< [in][release] pointer to memory to free ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -11706,7 +11706,7 @@ zeFabricVertexGetExp( ///< driver shall only retrieve that number of fabric vertices. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -11774,7 +11774,7 @@ zeFabricVertexGetSubVerticesExp( ///< driver shall only retrieve that number of sub-vertices. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -11830,7 +11830,7 @@ zeFabricVertexGetPropertiesExp( ze_fabric_vertex_exp_properties_t* pVertexProperties///< [in,out] query result for fabric vertex properties ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -11890,7 +11890,7 @@ zeFabricVertexGetDeviceExp( ze_device_handle_t* phDevice ///< [out] device handle corresponding to fabric vertex ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -11948,7 +11948,7 @@ zeDeviceGetFabricVertexExp( ze_fabric_vertex_handle_t* phVertex ///< [out] fabric vertex handle corresponding to device ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -12016,7 +12016,7 @@ zeFabricEdgeGetExp( ///< driver shall only retrieve that number of fabric edges. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -12076,7 +12076,7 @@ zeFabricEdgeGetVerticesExp( ze_fabric_vertex_handle_t* phVertexB ///< [out] fabric vertex connected to other end of the given fabric edge. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -12132,7 +12132,7 @@ zeFabricEdgeGetPropertiesExp( ze_fabric_edge_exp_properties_t* pEdgeProperties///< [in,out] query result for fabric edge properties ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -12222,7 +12222,7 @@ zeEventQueryKernelTimestampsExt( ///< available, the driver may only update the valid elements. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -12284,7 +12284,7 @@ zeRTASBuilderCreateExp( ze_rtas_builder_exp_handle_t* phBuilder ///< [out] handle of builder object ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -12346,7 +12346,7 @@ zeRTASBuilderGetBuildPropertiesExp( ze_rtas_builder_exp_properties_t* pProperties ///< [in,out] query result for builder properties ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -12408,7 +12408,7 @@ zeDriverRTASFormatCompatibilityCheckExp( ze_rtas_format_exp_t rtasFormatB ///< [in] operand B ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -12530,7 +12530,7 @@ zeRTASBuilderBuildExp( ///< bytes ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -12587,7 +12587,7 @@ zeRTASBuilderDestroyExp( ze_rtas_builder_exp_handle_t hBuilder ///< [in][release] handle of builder object to destroy ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -12646,7 +12646,7 @@ zeRTASParallelOperationCreateExp( ze_rtas_parallel_operation_exp_handle_t* phParallelOperation///< [out] handle of parallel operation object ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -12708,7 +12708,7 @@ zeRTASParallelOperationGetPropertiesExp( ze_rtas_parallel_operation_exp_properties_t* pProperties///< [in,out] query result for parallel operation properties ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -12761,7 +12761,7 @@ zeRTASParallelOperationJoinExp( ze_rtas_parallel_operation_exp_handle_t hParallelOperation ///< [in] handle of parallel operation object ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -12819,7 +12819,7 @@ zeRTASParallelOperationDestroyExp( ze_rtas_parallel_operation_exp_handle_t hParallelOperation ///< [in][release] handle of parallel operation object to destroy ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -12883,7 +12883,7 @@ zeMemGetPitchFor2dImage( size_t * rowPitch ///< [out] rowPitch ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -12942,7 +12942,7 @@ zeImageGetDeviceOffsetExp( uint64_t* pDeviceOffset ///< [out] bindless device offset for image ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -13009,7 +13009,7 @@ zeCommandListCreateCloneExp( ze_command_list_handle_t* phClonedCommandList ///< [out] pointer to handle of the cloned command list ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -13080,7 +13080,7 @@ zeCommandListImmediateAppendCommandListsExp( ///< of any appended command list(s) ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -13144,7 +13144,7 @@ zeCommandListGetNextCommandIdExp( uint64_t* pCommandId ///< [out] pointer to mutable command identifier to be written ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -13214,7 +13214,7 @@ zeCommandListGetNextCommandIdWithKernelsExp( uint64_t* pCommandId ///< [out] pointer to mutable command identifier to be written ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -13279,7 +13279,7 @@ zeCommandListUpdateMutableCommandsExp( ///< be chained via `pNext` member ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -13343,7 +13343,7 @@ zeCommandListUpdateMutableCommandSignalEventExp( ze_event_handle_t hSignalEvent ///< [in][optional] handle of the event to signal on completion ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -13416,7 +13416,7 @@ zeCommandListUpdateMutableCommandWaitEventsExp( ///< on before launching ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -13487,7 +13487,7 @@ zeCommandListUpdateMutableCommandKernelsExp( ///< identifier to switch to ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; diff --git a/source/lib/ze_libddi.cpp b/source/lib/ze_libddi.cpp index 2549ad93..502b2e61 100644 --- a/source/lib/ze_libddi.cpp +++ b/source/lib/ze_libddi.cpp @@ -8,7 +8,7 @@ * */ #include "ze_lib.h" -#ifndef DYNAMIC_LOAD_LOADER +#ifndef L0_STATIC_LOADER_BUILD #include "ze_ddi.h" #endif @@ -16,7 +16,7 @@ namespace ze_lib { /////////////////////////////////////////////////////////////////////////////// -#ifdef DYNAMIC_LOAD_LOADER +#ifdef L0_STATIC_LOADER_BUILD __zedlllocal ze_result_t context_t::zeDdiTableInit(ze_api_version_t version) { ze_result_t result = ZE_RESULT_SUCCESS; diff --git a/source/lib/zel_tracing_libddi.cpp b/source/lib/zel_tracing_libddi.cpp index f20b75bb..82f8817f 100644 --- a/source/lib/zel_tracing_libddi.cpp +++ b/source/lib/zel_tracing_libddi.cpp @@ -14,7 +14,7 @@ namespace ze_lib { /////////////////////////////////////////////////////////////////////////////// -#ifdef DYNAMIC_LOAD_LOADER +#ifdef L0_STATIC_LOADER_BUILD __zedlllocal ze_result_t context_t::zelTracingDdiTableInit(ze_api_version_t version) { ze_result_t result = ZE_RESULT_SUCCESS; diff --git a/source/lib/zes_libapi.cpp b/source/lib/zes_libapi.cpp index 11899ab1..5c0cb2e5 100644 --- a/source/lib/zes_libapi.cpp +++ b/source/lib/zes_libapi.cpp @@ -48,7 +48,7 @@ zesInit( ///< currently unused, must be 0 (default). ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD if (!ze_lib::context) { ze_lib::context = new ze_lib::context_t; } @@ -110,7 +110,7 @@ zesDriverGet( ///< loader shall only retrieve that number of sysman drivers. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -183,7 +183,7 @@ zesDriverGetExtensionProperties( ///< then driver shall only retrieve that number of extension properties. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -242,7 +242,7 @@ zesDriverGetExtensionFunctionAddress( void** ppFunctionAddress ///< [out] pointer to function pointer ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -311,7 +311,7 @@ zesDeviceGet( ///< driver shall only retrieve that number of sysman devices. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -367,7 +367,7 @@ zesDeviceGetProperties( zes_device_properties_t* pProperties ///< [in,out] Structure that will contain information about the device. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -424,7 +424,7 @@ zesDeviceGetState( zes_device_state_t* pState ///< [in,out] Structure that will contain information about the device. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -492,7 +492,7 @@ zesDeviceReset( ///< device will be forcibly killed. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -561,7 +561,7 @@ zesDeviceResetExt( zes_reset_properties_t* pProperties ///< [in] Device reset properties to apply ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -635,7 +635,7 @@ zesDeviceProcessesGetState( ///< number of processes. In this case, the return code will ::ZE_RESULT_ERROR_INVALID_SIZE. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -691,7 +691,7 @@ zesDevicePciGetProperties( zes_pci_properties_t* pProperties ///< [in,out] Will contain the PCI properties. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -747,7 +747,7 @@ zesDevicePciGetState( zes_pci_state_t* pState ///< [in,out] Will contain the PCI properties. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -811,7 +811,7 @@ zesDevicePciGetBars( ///< driver shall only retrieve information about that number of PCI bars. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -869,7 +869,7 @@ zesDevicePciGetStats( zes_pci_stats_t* pStats ///< [in,out] Will contain a snapshot of the latest stats. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -925,7 +925,7 @@ zesDeviceSetOverclockWaiver( zes_device_handle_t hDevice ///< [in] Sysman handle of the device. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -985,7 +985,7 @@ zesDeviceGetOverclockDomains( ///< doesn't support overclocking. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1049,7 +1049,7 @@ zesDeviceGetOverclockControls( ///< ::zes_overclock_control_t). ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1107,7 +1107,7 @@ zesDeviceResetOverclockSettings( ///< manufacturing state ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1174,7 +1174,7 @@ zesDeviceReadOverclockState( ze_bool_t* pPendingReset ///< [out] Pending reset 0 =manufacturing state, 1= shipped state).. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1240,7 +1240,7 @@ zesDeviceEnumOverclockDomains( ///< component handles. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1298,7 +1298,7 @@ zesOverclockGetDomainProperties( zes_overclock_properties_t* pDomainProperties ///< [in,out] The overclock properties for the specified domain. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1356,7 +1356,7 @@ zesOverclockGetDomainVFProperties( zes_vf_property_t* pVFProperties ///< [in,out] The VF min,max,step for a specified domain. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1417,7 +1417,7 @@ zesOverclockGetDomainControlProperties( zes_control_property_t* pControlProperties ///< [in,out] overclock control values. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1478,7 +1478,7 @@ zesOverclockGetControlCurrentValue( double* pValue ///< [in,out] Getting overclock control value for the specified control. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1540,7 +1540,7 @@ zesOverclockGetControlPendingValue( ///< format of the value depend on the control type. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1603,7 +1603,7 @@ zesOverclockSetControlUserValue( zes_pending_action_t* pPendingAction ///< [out] Pending overclock setting. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1666,7 +1666,7 @@ zesOverclockGetControlState( zes_pending_action_t* pPendingAction ///< [out] Pending overclock setting. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1732,7 +1732,7 @@ zesOverclockGetVFPointValues( ///< units from the custom V-F curve at the specified zero-based index ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1793,7 +1793,7 @@ zesOverclockSetVFPointValues( ///< custom V-F curve at the specified zero-based index ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1859,7 +1859,7 @@ zesDeviceEnumDiagnosticTestSuites( ///< component handles. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1916,7 +1916,7 @@ zesDiagnosticsGetProperties( ///< suite ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1984,7 +1984,7 @@ zesDiagnosticsGetTests( ///< driver shall only retrieve that number of tests. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2055,7 +2055,7 @@ zesDiagnosticsRunTests( zes_diag_result_t* pResult ///< [in,out] The result of the diagnostics ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2111,7 +2111,7 @@ zesDeviceEccAvailable( ze_bool_t* pAvailable ///< [out] ECC functionality is available (true)/unavailable (false). ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2167,7 +2167,7 @@ zesDeviceEccConfigurable( ze_bool_t* pConfigurable ///< [out] ECC can be enabled/disabled (true)/enabled/disabled (false). ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2223,7 +2223,7 @@ zesDeviceGetEccState( zes_device_ecc_properties_t* pState ///< [out] ECC state, pending state, and pending action for state change. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2287,7 +2287,7 @@ zesDeviceSetEccState( zes_device_ecc_properties_t* pState ///< [out] ECC state, pending state, and pending action for state change. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2353,7 +2353,7 @@ zesDeviceEnumEngineGroups( ///< component handles. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2409,7 +2409,7 @@ zesEngineGetProperties( zes_engine_properties_t* pProperties ///< [in,out] The properties for the specified engine group. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2468,7 +2468,7 @@ zesEngineGetActivity( ///< counters. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2524,7 +2524,7 @@ zesDeviceEventRegister( zes_event_type_flags_t events ///< [in] List of events to listen to. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2602,7 +2602,7 @@ zesDriverEventListen( ///< entry will be zero. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2680,7 +2680,7 @@ zesDriverEventListenEx( ///< entry will be zero. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2746,7 +2746,7 @@ zesDeviceEnumFabricPorts( ///< component handles. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2802,7 +2802,7 @@ zesFabricPortGetProperties( zes_fabric_port_properties_t* pProperties ///< [in,out] Will contain properties of the Fabric Port. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2859,7 +2859,7 @@ zesFabricPortGetLinkType( ///< port. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2915,7 +2915,7 @@ zesFabricPortGetConfig( zes_fabric_port_config_t* pConfig ///< [in,out] Will contain configuration of the Fabric Port. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2973,7 +2973,7 @@ zesFabricPortSetConfig( const zes_fabric_port_config_t* pConfig ///< [in] Contains new configuration of the Fabric Port. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3030,7 +3030,7 @@ zesFabricPortGetState( zes_fabric_port_state_t* pState ///< [in,out] Will contain the current state of the Fabric Port ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3088,7 +3088,7 @@ zesFabricPortGetThroughput( zes_fabric_port_throughput_t* pThroughput ///< [in,out] Will contain the Fabric port throughput counters. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3149,7 +3149,7 @@ zesFabricPortGetFabricErrorCounters( zes_fabric_port_error_counters_t* pErrors ///< [in,out] Will contain the Fabric port Error counters. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3210,7 +3210,7 @@ zesFabricPortGetMultiPortThroughput( ///< from multiple ports of type ::zes_fabric_port_throughput_t. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3276,7 +3276,7 @@ zesDeviceEnumFans( ///< component handles. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3332,7 +3332,7 @@ zesFanGetProperties( zes_fan_properties_t* pProperties ///< [in,out] Will contain the properties of the fan. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3389,7 +3389,7 @@ zesFanGetConfig( zes_fan_config_t* pConfig ///< [in,out] Will contain the current configuration of the fan. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3445,7 +3445,7 @@ zesFanSetDefaultMode( zes_fan_handle_t hFan ///< [in] Handle for the component. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3506,7 +3506,7 @@ zesFanSetFixedSpeedMode( const zes_fan_speed_t* speed ///< [in] The fixed fan speed setting ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3569,7 +3569,7 @@ zesFanSetSpeedTableMode( const zes_fan_speed_table_t* speedTable ///< [in] A table containing temperature/speed pairs. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3632,7 +3632,7 @@ zesFanGetState( ///< measured. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3698,7 +3698,7 @@ zesDeviceEnumFirmwares( ///< component handles. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3755,7 +3755,7 @@ zesFirmwareGetProperties( ///< firmware ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3818,7 +3818,7 @@ zesFirmwareFlash( uint32_t size ///< [in] Size of the flash image. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3874,7 +3874,7 @@ zesFirmwareGetFlashProgress( uint32_t* pCompletionPercent ///< [in,out] Pointer to the Completion Percentage of Firmware Update ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3934,7 +3934,7 @@ zesFirmwareGetConsoleLogs( char* pFirmwareLog ///< [in,out][optional] pointer to null-terminated string of the log. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4000,7 +4000,7 @@ zesDeviceEnumFrequencyDomains( ///< component handles. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4056,7 +4056,7 @@ zesFrequencyGetProperties( zes_freq_properties_t* pProperties ///< [in,out] The frequency properties for the specified domain. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4123,7 +4123,7 @@ zesFrequencyGetAvailableClocks( ///< then the driver shall only retrieve that number of frequencies. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4180,7 +4180,7 @@ zesFrequencyGetRange( ///< specified domain. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4242,7 +4242,7 @@ zesFrequencySetRange( ///< specified domain. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4299,7 +4299,7 @@ zesFrequencyGetState( zes_freq_state_t* pState ///< [in,out] Frequency state for the specified domain. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4356,7 +4356,7 @@ zesFrequencyGetThrottleTime( ///< specified domain. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4413,7 +4413,7 @@ zesFrequencyOcGetCapabilities( zes_oc_capabilities_t* pOcCapabilities ///< [in,out] Pointer to the capabilities structure. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4482,7 +4482,7 @@ zesFrequencyOcGetFrequencyTarget( ///< ::zes_oc_capabilities_t. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4549,7 +4549,7 @@ zesFrequencyOcSetFrequencyTarget( ///< ::zes_oc_capabilities_t. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4620,7 +4620,7 @@ zesFrequencyOcGetVoltageTarget( ///< `maxOcVoltageOffset` members of ::zes_oc_capabilities_t. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4688,7 +4688,7 @@ zesFrequencyOcSetVoltageTarget( ///< `maxOcVoltageOffset` members of ::zes_oc_capabilities_t. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4753,7 +4753,7 @@ zesFrequencyOcSetMode( zes_oc_mode_t CurrentOcMode ///< [in] Current Overclocking Mode ::zes_oc_mode_t. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4818,7 +4818,7 @@ zesFrequencyOcGetMode( zes_oc_mode_t* pCurrentOcMode ///< [out] Current Overclocking Mode ::zes_oc_mode_t. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4879,7 +4879,7 @@ zesFrequencyOcGetIccMax( ///< successful return. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4944,7 +4944,7 @@ zesFrequencyOcSetIccMax( double ocIccMax ///< [in] The new maximum current limit in Amperes. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5004,7 +5004,7 @@ zesFrequencyOcGetTjMax( ///< on successful return. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5069,7 +5069,7 @@ zesFrequencyOcSetTjMax( double ocTjMax ///< [in] The new maximum temperature limit in degrees Celsius. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5135,7 +5135,7 @@ zesDeviceEnumLeds( ///< component handles. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5191,7 +5191,7 @@ zesLedGetProperties( zes_led_properties_t* pProperties ///< [in,out] Will contain the properties of the LED. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5247,7 +5247,7 @@ zesLedGetState( zes_led_state_t* pState ///< [in,out] Will contain the current state of the LED. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5303,7 +5303,7 @@ zesLedSetState( ze_bool_t enable ///< [in] Set to TRUE to turn the LED on, FALSE to turn off. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5363,7 +5363,7 @@ zesLedSetColor( const zes_led_color_t* pColor ///< [in] New color of the LED. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5429,7 +5429,7 @@ zesDeviceEnumMemoryModules( ///< component handles. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5485,7 +5485,7 @@ zesMemoryGetProperties( zes_mem_properties_t* pProperties ///< [in,out] Will contain memory properties. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5541,7 +5541,7 @@ zesMemoryGetState( zes_mem_state_t* pState ///< [in,out] Will contain the current health and allocated memory. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5600,7 +5600,7 @@ zesMemoryGetBandwidth( ///< to memory, as well as the current maximum bandwidth. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5668,7 +5668,7 @@ zesDeviceEnumPerformanceFactorDomains( ///< component handles. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5725,7 +5725,7 @@ zesPerformanceFactorGetProperties( ///< Factor domain. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5782,7 +5782,7 @@ zesPerformanceFactorGetConfig( ///< hardware (may not be the same as the requested Performance Factor). ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5841,7 +5841,7 @@ zesPerformanceFactorSetConfig( double factor ///< [in] The new Performance Factor. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5907,7 +5907,7 @@ zesDeviceEnumPowerDomains( ///< component handles. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -5966,7 +5966,7 @@ zesDeviceGetCardPowerDomain( zes_pwr_handle_t* phPower ///< [in,out] power domain handle for the entire PCIe card. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -6022,7 +6022,7 @@ zesPowerGetProperties( zes_power_properties_t* pProperties ///< [in,out] Structure that will contain property data. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -6079,7 +6079,7 @@ zesPowerGetEnergyCounter( ///< timestamp when the last counter value was measured. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -6139,7 +6139,7 @@ zesPowerGetLimits( ///< power limits will not be returned. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -6203,7 +6203,7 @@ zesPowerSetLimits( ///< be made to the peak power limits. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -6264,7 +6264,7 @@ zesPowerGetEnergyThreshold( ///< enabled/energy threshold/process ID. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -6338,7 +6338,7 @@ zesPowerSetEnergyThreshold( double threshold ///< [in] The energy threshold to be set in joules. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -6404,7 +6404,7 @@ zesDeviceEnumPsus( ///< component handles. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -6460,7 +6460,7 @@ zesPsuGetProperties( zes_psu_properties_t* pProperties ///< [in,out] Will contain the properties of the power supply. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -6516,7 +6516,7 @@ zesPsuGetState( zes_psu_state_t* pState ///< [in,out] Will contain the current state of the power supply. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -6592,7 +6592,7 @@ zesDeviceEnumRasErrorSets( ///< component handles. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -6650,7 +6650,7 @@ zesRasGetProperties( zes_ras_properties_t* pProperties ///< [in,out] Structure describing RAS properties ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -6716,7 +6716,7 @@ zesRasGetConfig( ///< thresholds used to trigger events ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -6787,7 +6787,7 @@ zesRasSetConfig( const zes_ras_config_t* pConfig ///< [in] Change the RAS configuration - thresholds used to trigger events ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -6849,7 +6849,7 @@ zesRasGetState( zes_ras_state_t* pState ///< [in,out] Breakdown of where errors have occurred ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -6921,7 +6921,7 @@ zesDeviceEnumSchedulers( ///< component handles. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -6977,7 +6977,7 @@ zesSchedulerGetProperties( zes_sched_properties_t* pProperties ///< [in,out] Structure that will contain property data. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7035,7 +7035,7 @@ zesSchedulerGetCurrentMode( zes_sched_mode_t* pMode ///< [in,out] Will contain the current scheduler mode. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7095,7 +7095,7 @@ zesSchedulerGetTimeoutModeProperties( zes_sched_timeout_properties_t* pConfig ///< [in,out] Will contain the current parameters for this mode. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7155,7 +7155,7 @@ zesSchedulerGetTimesliceModeProperties( zes_sched_timeslice_properties_t* pConfig ///< [in,out] Will contain the current parameters for this mode. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7223,7 +7223,7 @@ zesSchedulerSetTimeoutMode( ///< apply the new scheduler mode. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7290,7 +7290,7 @@ zesSchedulerSetTimesliceMode( ///< apply the new scheduler mode. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7355,7 +7355,7 @@ zesSchedulerSetExclusiveMode( ///< apply the new scheduler mode. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7422,7 +7422,7 @@ zesSchedulerSetComputeUnitDebugMode( ///< apply the new scheduler mode. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7488,7 +7488,7 @@ zesDeviceEnumStandbyDomains( ///< component handles. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7544,7 +7544,7 @@ zesStandbyGetProperties( zes_standby_properties_t* pProperties ///< [in,out] Will contain the standby hardware properties. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7600,7 +7600,7 @@ zesStandbyGetMode( zes_standby_promo_mode_t* pMode ///< [in,out] Will contain the current standby mode. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7658,7 +7658,7 @@ zesStandbySetMode( zes_standby_promo_mode_t mode ///< [in] New standby mode. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7724,7 +7724,7 @@ zesDeviceEnumTemperatureSensors( ///< component handles. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7780,7 +7780,7 @@ zesTemperatureGetProperties( zes_temp_properties_t* pProperties ///< [in,out] Will contain the temperature sensor properties. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7842,7 +7842,7 @@ zesTemperatureGetConfig( zes_temp_config_t* pConfig ///< [in,out] Returns current configuration. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7921,7 +7921,7 @@ zesTemperatureSetConfig( const zes_temp_config_t* pConfig ///< [in] New configuration. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -7978,7 +7978,7 @@ zesTemperatureGetState( ///< in degrees Celsius. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -8044,7 +8044,7 @@ zesPowerGetLimitsExt( ///< number of components. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -8113,7 +8113,7 @@ zesPowerSetLimitsExt( zes_power_limit_ext_desc_t* pSustained ///< [in][optional][range(0, *pCount)] Array of power limit descriptors. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -8184,7 +8184,7 @@ zesEngineGetActivityExt( ///< of VF engine stats. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -8250,7 +8250,7 @@ zesRasGetStateExp( ///< shall only retrieve that number of RAS states. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -8313,7 +8313,7 @@ zesRasClearStateExp( zes_ras_error_category_exp_t category ///< [in] category for which error counter is to be cleared. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -8374,7 +8374,7 @@ zesFirmwareGetSecurityVersionExp( ///< returned if this property cannot be determined. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -8427,7 +8427,7 @@ zesFirmwareSetSecurityVersionExp( zes_firmware_handle_t hFirmware ///< [in] Handle for the component. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -8491,7 +8491,7 @@ zesDeviceGetSubDevicePropertiesExp( ///< the driver shall only retrieve that number of sub device property structures. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -8554,7 +8554,7 @@ zesDriverGetDeviceByUuidExp( uint32_t* subdeviceId ///< [out] If onSubdevice is true, this gives the ID of the sub-device ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -8621,7 +8621,7 @@ zesDeviceEnumActiveVFExp( ///< component handles. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -8679,7 +8679,7 @@ zesVFManagementGetVFPropertiesExp( zes_vf_exp_properties_t* pProperties ///< [in,out] Will contain VF properties. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -8750,7 +8750,7 @@ zesVFManagementGetVFMemoryUtilizationExp( ///< memory stats. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -8821,7 +8821,7 @@ zesVFManagementGetVFEngineUtilizationExp( ///< engine stats. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -8881,7 +8881,7 @@ zesVFManagementSetVFTelemetryModeExp( ze_bool_t enable ///< [in] Enable utilization telemetry. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -8941,7 +8941,7 @@ zesVFManagementSetVFTelemetrySamplingIntervalExp( uint64_t samplingInterval ///< [in] Sampling interval value. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -9007,7 +9007,7 @@ zesDeviceEnumEnabledVFExp( ///< component handles. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -9065,7 +9065,7 @@ zesVFManagementGetVFCapabilitiesExp( zes_vf_exp_capabilities_t* pCapability ///< [in,out] Will contain VF capability. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -9133,7 +9133,7 @@ zesVFManagementGetVFMemoryUtilizationExp2( ///< memory stats. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -9201,7 +9201,7 @@ zesVFManagementGetVFEngineUtilizationExp2( ///< engine stats. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -9257,7 +9257,7 @@ zesVFManagementGetVFCapabilitiesExp2( zes_vf_exp2_capabilities_t* pCapability ///< [in,out] Will contain VF capability. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; diff --git a/source/lib/zes_libddi.cpp b/source/lib/zes_libddi.cpp index 05f2e0e4..f6e85b0b 100644 --- a/source/lib/zes_libddi.cpp +++ b/source/lib/zes_libddi.cpp @@ -8,7 +8,7 @@ * */ #include "ze_lib.h" -#ifndef DYNAMIC_LOAD_LOADER +#ifndef L0_STATIC_LOADER_BUILD #include "zes_ddi.h" #endif @@ -16,7 +16,7 @@ namespace ze_lib { /////////////////////////////////////////////////////////////////////////////// -#ifdef DYNAMIC_LOAD_LOADER +#ifdef L0_STATIC_LOADER_BUILD __zedlllocal ze_result_t context_t::zesDdiTableInit(ze_api_version_t version) { ze_result_t result = ZE_RESULT_SUCCESS; diff --git a/source/lib/zet_libapi.cpp b/source/lib/zet_libapi.cpp index fb8377b2..8f10a5d6 100644 --- a/source/lib/zet_libapi.cpp +++ b/source/lib/zet_libapi.cpp @@ -44,7 +44,7 @@ zetModuleGetDebugInfo( uint8_t* pDebugInfo ///< [in,out][optional] byte pointer to debug info ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -96,7 +96,7 @@ zetDeviceGetDebugProperties( zet_device_debug_properties_t* pDebugProperties ///< [in,out] query result for debug properties ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -160,7 +160,7 @@ zetDebugAttach( zet_debug_session_handle_t* phDebug ///< [out] debug session handle ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -209,7 +209,7 @@ zetDebugDetach( zet_debug_session_handle_t hDebug ///< [in][release] debug session handle ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -270,7 +270,7 @@ zetDebugReadEvent( zet_debug_event_t* event ///< [in,out] a pointer to a ::zet_debug_event_t. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -322,7 +322,7 @@ zetDebugAcknowledgeEvent( const zet_debug_event_t* event ///< [in] a pointer to a ::zet_debug_event_t. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -374,7 +374,7 @@ zetDebugInterrupt( ze_device_thread_t thread ///< [in] the thread to interrupt ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -426,7 +426,7 @@ zetDebugResume( ze_device_thread_t thread ///< [in] the thread to resume ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -491,7 +491,7 @@ zetDebugReadMemory( void* buffer ///< [in,out] a buffer to hold a copy of the memory ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -556,7 +556,7 @@ zetDebugWriteMemory( const void* buffer ///< [in] a buffer holding the pattern to write ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -617,7 +617,7 @@ zetDebugGetRegisterSetProperties( ///< then driver shall only retrieve that number of register set properties. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -683,7 +683,7 @@ zetDebugGetThreadRegisterSetProperties( ///< then driver shall only retrieve that number of register set properties. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -743,7 +743,7 @@ zetDebugReadRegisters( void* pRegisterValues ///< [in,out][optional][range(0, count)] buffer of register values ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -803,7 +803,7 @@ zetDebugWriteRegisters( void* pRegisterValues ///< [in,out][optional][range(0, count)] buffer of register values ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -866,7 +866,7 @@ zetMetricGroupGet( ///< driver shall only retrieve that number of metric groups. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -921,7 +921,7 @@ zetMetricGroupGetProperties( zet_metric_group_properties_t* pProperties ///< [in,out] metric group properties ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -990,7 +990,7 @@ zetMetricGroupCalculateMetricValues( ///< then driver shall only calculate that number of metric values. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1052,7 +1052,7 @@ zetMetricGet( ///< shall only retrieve that number of metrics. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1107,7 +1107,7 @@ zetMetricGetProperties( zet_metric_properties_t* pProperties ///< [in,out] metric properties ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1180,7 +1180,7 @@ zetContextActivateMetricGroups( ///< metric query and metric stream must use activated metric groups. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1250,7 +1250,7 @@ zetMetricStreamerOpen( zet_metric_streamer_handle_t* phMetricStreamer ///< [out] handle of metric streamer ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1312,7 +1312,7 @@ zetCommandListAppendMetricStreamerMarker( uint32_t value ///< [in] streamer marker value ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1365,7 +1365,7 @@ zetMetricStreamerClose( zet_metric_streamer_handle_t hMetricStreamer ///< [in][release] handle of the metric streamer ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1432,7 +1432,7 @@ zetMetricStreamerReadData( ///< reports in raw format ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1496,7 +1496,7 @@ zetMetricQueryPoolCreate( zet_metric_query_pool_handle_t* phMetricQueryPool ///< [out] handle of metric query pool ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1555,7 +1555,7 @@ zetMetricQueryPoolDestroy( zet_metric_query_pool_handle_t hMetricQueryPool ///< [in][release] handle of the metric query pool ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1612,7 +1612,7 @@ zetMetricQueryCreate( zet_metric_query_handle_t* phMetricQuery ///< [out] handle of metric query ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1669,7 +1669,7 @@ zetMetricQueryDestroy( zet_metric_query_handle_t hMetricQuery ///< [in][release] handle of metric query ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1724,7 +1724,7 @@ zetMetricQueryReset( zet_metric_query_handle_t hMetricQuery ///< [in] handle of metric query ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1785,7 +1785,7 @@ zetCommandListAppendMetricQueryBegin( zet_metric_query_handle_t hMetricQuery ///< [in] handle of the metric query ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1860,7 +1860,7 @@ zetCommandListAppendMetricQueryEnd( ze_event_handle_t* phWaitEvents ///< [in][mbz] must be nullptr ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1913,7 +1913,7 @@ zetCommandListAppendMetricMemoryBarrier( zet_command_list_handle_t hCommandList ///< [in] handle of the command list ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -1976,7 +1976,7 @@ zetMetricQueryGetData( ///< reports in raw format ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2036,7 +2036,7 @@ zetKernelGetProfileInfo( zet_profile_properties_t* pProfileProperties ///< [out] pointer to profile properties ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2098,7 +2098,7 @@ zetTracerExpCreate( zet_tracer_exp_handle_t* phTracer ///< [out] pointer to handle of tracer object created ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2156,7 +2156,7 @@ zetTracerExpDestroy( zet_tracer_exp_handle_t hTracer ///< [in][release] handle of tracer object to destroy ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2217,7 +2217,7 @@ zetTracerExpSetPrologues( zet_core_callbacks_t* pCoreCbs ///< [in] pointer to table of 'core' callback function pointers ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2278,7 +2278,7 @@ zetTracerExpSetEpilogues( zet_core_callbacks_t* pCoreCbs ///< [in] pointer to table of 'core' callback function pointers ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2332,7 +2332,7 @@ zetTracerExpSetEnabled( ze_bool_t enable ///< [in] enable the tracer if true; disable if false ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2394,7 +2394,7 @@ zetDeviceGetConcurrentMetricGroupsExp( ///< replays necessary. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2472,7 +2472,7 @@ zetMetricTracerCreateExp( zet_metric_tracer_exp_handle_t* phMetricTracer ///< [out] handle of the metric tracer ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2525,7 +2525,7 @@ zetMetricTracerDestroyExp( zet_metric_tracer_exp_handle_t hMetricTracer ///< [in] handle of the metric tracer ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2586,7 +2586,7 @@ zetMetricTracerEnableExp( ///< when the tracer is active. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2648,7 +2648,7 @@ zetMetricTracerDisableExp( ///< has no more data to be retrieved. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2718,7 +2718,7 @@ zetMetricTracerReadDataExp( ///< data in raw format ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2770,7 +2770,7 @@ zetMetricDecoderCreateExp( zet_metric_decoder_exp_handle_t* phMetricDecoder///< [out] handle of the metric decoder object ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2819,7 +2819,7 @@ zetMetricDecoderDestroyExp( zet_metric_decoder_exp_handle_t phMetricDecoder ///< [in] handle of the metric decoder object ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2890,7 +2890,7 @@ zetMetricDecoderGetDecodableMetricsExp( ///< the hMetricDecoder handle provided. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -2983,7 +2983,7 @@ zetMetricTracerDecodeExp( ///< decoded metric entries ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3042,7 +3042,7 @@ zetCommandListAppendMarkerExp( uint32_t value ///< [in] marker value ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3104,7 +3104,7 @@ zetDeviceEnableMetricsExp( zet_device_handle_t hDevice ///< [in] handle of the device where metrics collection has to be enabled. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3163,7 +3163,7 @@ zetDeviceDisableMetricsExp( zet_device_handle_t hDevice ///< [in] handle of the device where metrics collection has to be disabled ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3251,7 +3251,7 @@ zetMetricGroupCalculateMultipleMetricValuesExp( ///< then driver shall only calculate that number of metric values. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3312,7 +3312,7 @@ zetMetricGroupGetGlobalTimestampsExp( uint64_t* metricTimestamp ///< [out] Metric timestamp. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3381,7 +3381,7 @@ zetMetricGroupGetExportDataExp( uint8_t * pExportData ///< [in,out][optional][range(0, *pExportDataSize)] buffer of exported data. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3470,7 +3470,7 @@ zetMetricGroupCalculateMetricExportDataExp( ///< then driver shall only calculate that number of metric values. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3535,7 +3535,7 @@ zetMetricProgrammableGetExp( ///< then driver shall only retrieve that number of metric programmables. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3590,7 +3590,7 @@ zetMetricProgrammableGetPropertiesExp( zet_metric_programmable_exp_properties_t* pProperties ///< [in,out] properties of the metric programmable ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3654,7 +3654,7 @@ zetMetricProgrammableGetParamInfoExp( ///< then driver shall only retrieve that number of parameter info. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3720,7 +3720,7 @@ zetMetricProgrammableGetParamValueInfoExp( ///< then driver shall only retrieve that number of value info. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3802,7 +3802,7 @@ zetMetricCreateFromProgrammableExp2( ///< shall only retrieve that number of metric handles. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3877,7 +3877,7 @@ zetMetricCreateFromProgrammableExp( ///< shall only retrieve that number of metric handles. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -3957,7 +3957,7 @@ zetDeviceCreateMetricGroupsFromMetricsExp( ///< Created Metric group handles. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4023,7 +4023,7 @@ zetMetricGroupCreateExp( zet_metric_group_handle_t* phMetricGroup ///< [in,out] Created Metric group handle ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4097,7 +4097,7 @@ zetMetricGroupAddMetricExp( ///< available, then driver shall only retrieve that length of error string. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4157,7 +4157,7 @@ zetMetricGroupRemoveMetricExp( zet_metric_handle_t hMetric ///< [in] Metric handle to be removed from the metric group. ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4226,7 +4226,7 @@ zetMetricGroupCloseExp( zet_metric_group_handle_t hMetricGroup ///< [in] Handle of the metric group ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4289,7 +4289,7 @@ zetMetricGroupDestroyExp( zet_metric_group_handle_t hMetricGroup ///< [in] Handle of the metric group to destroy ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; @@ -4346,7 +4346,7 @@ zetMetricDestroyExp( zet_metric_handle_t hMetric ///< [in] Handle of the metric to destroy ) { - #ifdef DYNAMIC_LOAD_LOADER + #ifdef L0_STATIC_LOADER_BUILD ze_result_t result = ZE_RESULT_SUCCESS; if(ze_lib::destruction) { return ZE_RESULT_ERROR_UNINITIALIZED; diff --git a/source/lib/zet_libddi.cpp b/source/lib/zet_libddi.cpp index af6143c5..2109d01d 100644 --- a/source/lib/zet_libddi.cpp +++ b/source/lib/zet_libddi.cpp @@ -8,7 +8,7 @@ * */ #include "ze_lib.h" -#ifndef DYNAMIC_LOAD_LOADER +#ifndef L0_STATIC_LOADER_BUILD #include "zet_ddi.h" #endif @@ -16,7 +16,7 @@ namespace ze_lib { /////////////////////////////////////////////////////////////////////////////// -#ifdef DYNAMIC_LOAD_LOADER +#ifdef L0_STATIC_LOADER_BUILD __zedlllocal ze_result_t context_t::zetDdiTableInit(ze_api_version_t version) { ze_result_t result = ZE_RESULT_SUCCESS; diff --git a/source/loader/linux/loader_init.cpp b/source/loader/linux/loader_init.cpp index aa9f57ba..67c6456d 100644 --- a/source/loader/linux/loader_init.cpp +++ b/source/loader/linux/loader_init.cpp @@ -10,7 +10,7 @@ namespace loader { -#ifndef DYNAMIC_LOAD_LOADER +#ifndef L0_STATIC_LOADER_BUILD void __attribute__((constructor)) createLoaderContext() { context = new context_t; } diff --git a/source/loader/windows/loader_init.cpp b/source/loader/windows/loader_init.cpp index 03baad8a..2d3bba32 100644 --- a/source/loader/windows/loader_init.cpp +++ b/source/loader/windows/loader_init.cpp @@ -10,7 +10,7 @@ namespace loader { -#ifdef DYNAMIC_LOAD_LOADER +#ifdef L0_STATIC_LOADER_BUILD extern "C" BOOL APIENTRY DllMain(HINSTANCE hinstDLL, DWORD fdwReason, LPVOID lpvReserved) { if (fdwReason == DLL_PROCESS_DETACH) { delete context;