From 618f1dd346c8316445ab6f3991b9efb69e8cae57 Mon Sep 17 00:00:00 2001 From: Aravind Gopalakrishnan Date: Wed, 14 Feb 2024 12:55:20 +0000 Subject: [PATCH] feature: Implement zeCommandListImmediateAppendCommandListsExp [1/N] Prepare execute call to accept event args Related-To: NEO-10356 Signed-off-by: Aravind Gopalakrishnan --- .../api/core/ze_cmdqueue_api_entrypoints.h | 2 +- level_zero/core/source/cmdlist/cmdlist_hw.inl | 2 +- level_zero/core/source/cmdqueue/cmdqueue.h | 4 +- level_zero/core/source/cmdqueue/cmdqueue_hw.h | 12 ++- .../core/source/cmdqueue/cmdqueue_hw.inl | 17 +++- level_zero/core/source/device/device_imp.cpp | 2 +- .../test/aub_tests/aub_hello_world_test.cpp | 4 +- .../bindless/bindless_kernel_aub_tests.cpp | 4 +- .../append_kernel_indirect_aub_tests.cpp | 10 +- .../aub_tests/debugger/debugger_aub_tests.cpp | 4 +- .../unit_tests/fixtures/cmdlist_fixture.inl | 32 +++---- ...dqueue_thread_arbitration_policy_gen11.cpp | 8 +- .../test_cmdqueue_enqueuecommandlist_gen9.cpp | 10 +- .../unit_tests/gen9/test_cmdqueue_gen9.cpp | 8 +- .../test/unit_tests/mocks/mock_cmdqueue.h | 4 +- .../linux/cmdqueue_linux_tests.cpp | 4 +- .../unit_tests/sources/assert/test_assert.cpp | 4 +- .../sources/cmdlist/test_cmdlist_2.cpp | 26 ++--- .../sources/cmdlist/test_cmdlist_3.cpp | 4 +- .../sources/cmdlist/test_cmdlist_5.cpp | 40 ++++---- .../sources/cmdlist/test_cmdlist_6.cpp | 24 ++--- .../sources/cmdlist/test_cmdlist_7.cpp | 8 +- .../test_cmdlist_append_launch_kernel_1.cpp | 6 +- .../cmdlist/test_cmdlist_xehp_and_later.cpp | 10 +- .../sources/cmdlist/test_in_order_cmdlist.cpp | 70 +++++++------- .../sources/cmdqueue/test_cmdqueue_1.cpp | 96 +++++++++---------- .../sources/cmdqueue/test_cmdqueue_2.cpp | 16 ++-- .../sources/cmdqueue/test_cmdqueue_3.cpp | 38 ++++---- .../cmdqueue/test_cmdqueue_debugger.cpp | 4 +- .../test_cmdqueue_enqueue_cmdlist.cpp | 46 ++++----- .../test_cmdqueue_enqueue_cmdlist_2.cpp | 24 ++--- .../sources/context/test_context.cpp | 6 +- .../sources/debugger/test_l0_debugger_1.cpp | 12 +-- .../sources/debugger/test_l0_debugger_2.cpp | 8 +- .../test_l0_debugger_sba_tracking.cpp | 12 +-- .../sources/device/test_l0_device.cpp | 12 ++- .../xe_hpc_core/test_cmdlist_xe_hpc_core.cpp | 12 +-- .../xe_hpc_core/test_cmdqueue_xe_hpc_core.cpp | 8 +- ...mdqueue_enqueuecommandlist_xe_hpg_core.cpp | 6 +- 39 files changed, 320 insertions(+), 299 deletions(-) diff --git a/level_zero/api/core/ze_cmdqueue_api_entrypoints.h b/level_zero/api/core/ze_cmdqueue_api_entrypoints.h index 8bc10b4f24..01c943d419 100644 --- a/level_zero/api/core/ze_cmdqueue_api_entrypoints.h +++ b/level_zero/api/core/ze_cmdqueue_api_entrypoints.h @@ -30,7 +30,7 @@ ze_result_t zeCommandQueueExecuteCommandLists( uint32_t numCommandLists, ze_command_list_handle_t *phCommandLists, ze_fence_handle_t hFence) { - return L0::CommandQueue::fromHandle(hCommandQueue)->executeCommandLists(numCommandLists, phCommandLists, hFence, true); + return L0::CommandQueue::fromHandle(hCommandQueue)->executeCommandLists(numCommandLists, phCommandLists, hFence, true, nullptr, 0, nullptr); } ze_result_t zeCommandQueueSynchronize( diff --git a/level_zero/core/source/cmdlist/cmdlist_hw.inl b/level_zero/core/source/cmdlist/cmdlist_hw.inl index 9270471e18..53d091c090 100644 --- a/level_zero/core/source/cmdlist/cmdlist_hw.inl +++ b/level_zero/core/source/cmdlist/cmdlist_hw.inl @@ -307,7 +307,7 @@ inline ze_result_t CommandListCoreFamily::executeCommandListImmed ze_command_list_handle_t immediateHandle = this->toHandle(); this->commandContainer.removeDuplicatesFromResidencyContainer(); - const auto commandListExecutionResult = cmdQImmediate->executeCommandLists(1, &immediateHandle, nullptr, performMigration); + const auto commandListExecutionResult = cmdQImmediate->executeCommandLists(1, &immediateHandle, nullptr, performMigration, nullptr, 0, nullptr); if (commandListExecutionResult == ZE_RESULT_ERROR_DEVICE_LOST) { return commandListExecutionResult; } diff --git a/level_zero/core/source/cmdqueue/cmdqueue.h b/level_zero/core/source/cmdqueue/cmdqueue.h index fc5fcdcc90..31acd72c0e 100644 --- a/level_zero/core/source/cmdqueue/cmdqueue.h +++ b/level_zero/core/source/cmdqueue/cmdqueue.h @@ -43,7 +43,9 @@ struct CommandQueue : _ze_command_queue_handle_t { virtual ze_result_t destroy() = 0; virtual ze_result_t executeCommandLists(uint32_t numCommandLists, ze_command_list_handle_t *phCommandLists, - ze_fence_handle_t hFence, bool performMigration) = 0; + ze_fence_handle_t hFence, bool performMigration, + ze_event_handle_t hSignalEvent, uint32_t numWaitEvents, + ze_event_handle_t *phWaitEvents) = 0; virtual ze_result_t executeCommands(uint32_t numCommands, void *phCommands, ze_fence_handle_t hFence) = 0; diff --git a/level_zero/core/source/cmdqueue/cmdqueue_hw.h b/level_zero/core/source/cmdqueue/cmdqueue_hw.h index 354e4f31b1..fcdf007b2d 100644 --- a/level_zero/core/source/cmdqueue/cmdqueue_hw.h +++ b/level_zero/core/source/cmdqueue/cmdqueue_hw.h @@ -27,7 +27,9 @@ struct CommandQueueHw : public CommandQueueImp { ze_result_t createFence(const ze_fence_desc_t *desc, ze_fence_handle_t *phFence) override; ze_result_t executeCommandLists(uint32_t numCommandLists, ze_command_list_handle_t *phCommandLists, - ze_fence_handle_t hFence, bool performMigration) override; + ze_fence_handle_t hFence, bool performMigration, + ze_event_handle_t hSignalEvent, uint32_t numWaitEvents, + ze_event_handle_t *phWaitEvents) override; ze_result_t executeCommands(uint32_t numCommands, void *phCommands, ze_fence_handle_t hFence) override; @@ -112,11 +114,15 @@ struct CommandQueueHw : public CommandQueueImp { ze_result_t executeCommandListsRegular(CommandListExecutionContext &ctx, uint32_t numCommandLists, ze_command_list_handle_t *commandListHandles, - ze_fence_handle_t hFence); + ze_fence_handle_t hFence, + ze_event_handle_t hSignalEvent, uint32_t numWaitEvents, + ze_event_handle_t *phWaitEvents); inline ze_result_t executeCommandListsCopyOnly(CommandListExecutionContext &ctx, uint32_t numCommandLists, ze_command_list_handle_t *phCommandLists, - ze_fence_handle_t hFence); + ze_fence_handle_t hFence, + ze_event_handle_t hSignalEvent, uint32_t numWaitEvents, + ze_event_handle_t *phWaitEvents); inline size_t computeDebuggerCmdsSize(const CommandListExecutionContext &ctx); inline size_t computePreemptionSizeForCommandList(CommandListExecutionContext &ctx, CommandList *commandList, diff --git a/level_zero/core/source/cmdqueue/cmdqueue_hw.inl b/level_zero/core/source/cmdqueue/cmdqueue_hw.inl index deb58c8e4f..bf76e3b0b7 100644 --- a/level_zero/core/source/cmdqueue/cmdqueue_hw.inl +++ b/level_zero/core/source/cmdqueue/cmdqueue_hw.inl @@ -58,7 +58,10 @@ ze_result_t CommandQueueHw::executeCommandLists( uint32_t numCommandLists, ze_command_list_handle_t *phCommandLists, ze_fence_handle_t hFence, - bool performMigration) { + bool performMigration, + ze_event_handle_t hSignalEvent, + uint32_t numWaitEvents, + ze_event_handle_t *phWaitEvents) { auto ret = ZE_RESULT_SUCCESS; @@ -86,9 +89,9 @@ ze_result_t CommandQueueHw::executeCommandLists( this->device->activateMetricGroups(); if (this->isCopyOnlyCommandQueue) { - ret = this->executeCommandListsCopyOnly(ctx, numCommandLists, phCommandLists, hFence); + ret = this->executeCommandListsCopyOnly(ctx, numCommandLists, phCommandLists, hFence, nullptr, 0, nullptr); } else { - ret = this->executeCommandListsRegular(ctx, numCommandLists, phCommandLists, hFence); + ret = this->executeCommandListsRegular(ctx, numCommandLists, phCommandLists, hFence, nullptr, 0, nullptr); } if (NEO::debugManager.flags.PauseOnEnqueue.get() != -1) { @@ -103,7 +106,9 @@ ze_result_t CommandQueueHw::executeCommandListsRegular( CommandListExecutionContext &ctx, uint32_t numCommandLists, ze_command_list_handle_t *commandListHandles, - ze_fence_handle_t hFence) { + ze_fence_handle_t hFence, + ze_event_handle_t hSignalEvent, uint32_t numWaitEvents, + ze_event_handle_t *phWaitEvents) { this->setupCmdListsAndContextParams(ctx, commandListHandles, numCommandLists, hFence); ctx.isDirectSubmissionEnabled = this->csr->isDirectSubmissionEnabled(); @@ -258,7 +263,9 @@ ze_result_t CommandQueueHw::executeCommandListsCopyOnly( CommandListExecutionContext &ctx, uint32_t numCommandLists, ze_command_list_handle_t *phCommandLists, - ze_fence_handle_t hFence) { + ze_fence_handle_t hFence, + ze_event_handle_t hSignalEvent, uint32_t numWaitEvents, + ze_event_handle_t *phWaitEvents) { this->setupCmdListsAndContextParams(ctx, phCommandLists, numCommandLists, hFence); ctx.isDirectSubmissionEnabled = this->csr->isBlitterDirectSubmissionEnabled(); diff --git a/level_zero/core/source/device/device_imp.cpp b/level_zero/core/source/device/device_imp.cpp index 27bdcc1867..338e3edc50 100644 --- a/level_zero/core/source/device/device_imp.cpp +++ b/level_zero/core/source/device/device_imp.cpp @@ -154,7 +154,7 @@ ze_result_t DeviceImp::submitCopyForP2P(ze_device_handle_t hPeerDevice, ze_bool_ L0::CommandList::fromHandle(commandList)->close(); if (ret == ZE_RESULT_SUCCESS) { - ret = L0::CommandQueue::fromHandle(commandQueue)->executeCommandLists(1, &commandList, nullptr, true); + ret = L0::CommandQueue::fromHandle(commandQueue)->executeCommandLists(1, &commandList, nullptr, true, nullptr, 0, nullptr); if (ret == ZE_RESULT_SUCCESS) { this->crossAccessEnabledDevices[peerRootDeviceIndex] = true; pPeerDevice->crossAccessEnabledDevices[this->getNEODevice()->getRootDeviceIndex()] = true; diff --git a/level_zero/core/test/aub_tests/aub_hello_world_test.cpp b/level_zero/core/test/aub_tests/aub_hello_world_test.cpp index 29a7922654..a370467cc9 100644 --- a/level_zero/core/test/aub_tests/aub_hello_world_test.cpp +++ b/level_zero/core/test/aub_tests/aub_hello_world_test.cpp @@ -1,5 +1,5 @@ /* - * Copyright (C) 2021-2023 Intel Corporation + * Copyright (C) 2021-2024 Intel Corporation * * SPDX-License-Identifier: MIT * @@ -36,7 +36,7 @@ TEST_F(AUBHelloWorldL0, whenAppendMemoryCopyIsCalledThenMemoryIsProperlyCopied) commandList->close(); auto pHCmdList = std::make_unique(commandList->toHandle()); - pCmdq->executeCommandLists(1, pHCmdList.get(), nullptr, false); + pCmdq->executeCommandLists(1, pHCmdList.get(), nullptr, false, nullptr, 0, nullptr); pCmdq->synchronize(std::numeric_limits::max()); EXPECT_TRUE(csr->expectMemory(dstMemory, srcMemory, size, AubMemDump::CmdServicesMemTraceMemoryCompare::CompareOperationValues::CompareEqual)); diff --git a/level_zero/core/test/aub_tests/bindless/bindless_kernel_aub_tests.cpp b/level_zero/core/test/aub_tests/bindless/bindless_kernel_aub_tests.cpp index 2b1a357ff7..e8ec0236fd 100644 --- a/level_zero/core/test/aub_tests/bindless/bindless_kernel_aub_tests.cpp +++ b/level_zero/core/test/aub_tests/bindless/bindless_kernel_aub_tests.cpp @@ -1,5 +1,5 @@ /* - * Copyright (C) 2021-2023 Intel Corporation + * Copyright (C) 2021-2024 Intel Corporation * * SPDX-License-Identifier: MIT * @@ -106,7 +106,7 @@ HWTEST_F(L0BindlessAub, DISABLED_GivenBindlessKernelWhenExecutedThenOutputIsCorr EXPECT_EQ(ZE_RESULT_SUCCESS, zeCommandListAppendLaunchKernel(cmdListHandle, kernel, &dispatchTraits, nullptr, 0, nullptr)); commandList->close(); - pCmdq->executeCommandLists(1, &cmdListHandle, nullptr, false); + pCmdq->executeCommandLists(1, &cmdListHandle, nullptr, false, nullptr, 0, nullptr); pCmdq->synchronize(std::numeric_limits::max()); expectMemory(reinterpret_cast(driverHandle->svmAllocsManager->getSVMAlloc(bufferDst)->gpuAllocations.getDefaultGraphicsAllocation()->getGpuAddress()), diff --git a/level_zero/core/test/aub_tests/cmdlist/append_kernel_indirect_aub_tests.cpp b/level_zero/core/test/aub_tests/cmdlist/append_kernel_indirect_aub_tests.cpp index 8b2e20a07b..3ee752c351 100644 --- a/level_zero/core/test/aub_tests/cmdlist/append_kernel_indirect_aub_tests.cpp +++ b/level_zero/core/test/aub_tests/cmdlist/append_kernel_indirect_aub_tests.cpp @@ -1,5 +1,5 @@ /* - * Copyright (C) 2021-2023 Intel Corporation + * Copyright (C) 2021-2024 Intel Corporation * * SPDX-License-Identifier: MIT * @@ -85,7 +85,7 @@ TEST_F(AUBAppendKernelIndirectL0, whenAppendKernelIndirectThenGlobalWorkSizeIsPr EXPECT_EQ(ZE_RESULT_SUCCESS, zeCommandListAppendLaunchKernelIndirect(cmdListHandle, kernel, &dispatchTraits, nullptr, 0, nullptr)); commandList->close(); - pCmdq->executeCommandLists(1, &cmdListHandle, nullptr, false); + pCmdq->executeCommandLists(1, &cmdListHandle, nullptr, false, nullptr, 0, nullptr); pCmdq->synchronize(std::numeric_limits::max()); EXPECT_TRUE(csr->expectMemory(outBuffer, expectedGlobalWorkSize, size, AubMemDump::CmdServicesMemTraceMemoryCompare::CompareOperationValues::CompareEqual)); @@ -130,7 +130,7 @@ TEST_F(AUBAppendKernelIndirectL0, whenAppendKernelIndirectThenGroupCountIsProper EXPECT_EQ(ZE_RESULT_SUCCESS, zeCommandListAppendLaunchKernelIndirect(cmdListHandle, kernel, &dispatchTraits, nullptr, 0, nullptr)); commandList->close(); - pCmdq->executeCommandLists(1, &cmdListHandle, nullptr, false); + pCmdq->executeCommandLists(1, &cmdListHandle, nullptr, false, nullptr, 0, nullptr); pCmdq->synchronize(std::numeric_limits::max()); EXPECT_TRUE(csr->expectMemory(outBuffer, groupCount, size, AubMemDump::CmdServicesMemTraceMemoryCompare::CompareOperationValues::CompareEqual)); @@ -190,7 +190,7 @@ TEST_F(AUBAppendKernelIndirectL0, whenAppendMultipleKernelsIndirectThenGroupCoun EXPECT_EQ(ZE_RESULT_SUCCESS, zeCommandListAppendLaunchMultipleKernelsIndirect(cmdListHandle, 2, kernels, kernelCount, dispatchTraits, nullptr, 0, nullptr)); commandList->close(); - pCmdq->executeCommandLists(1, &cmdListHandle, nullptr, false); + pCmdq->executeCommandLists(1, &cmdListHandle, nullptr, false, nullptr, 0, nullptr); pCmdq->synchronize(std::numeric_limits::max()); EXPECT_TRUE(csr->expectMemory(outBuffer, groupCount, size, AubMemDump::CmdServicesMemTraceMemoryCompare::CompareOperationValues::CompareEqual)); @@ -263,7 +263,7 @@ TEST_F(AUBAppendKernelIndirectL0, whenAppendKernelIndirectThenWorkDimIsProperlyP EXPECT_EQ(ZE_RESULT_SUCCESS, zeCommandListAppendLaunchKernelIndirect(cmdListHandle, kernel, &dispatchTraits, nullptr, 0, nullptr)); commandList->close(); - pCmdq->executeCommandLists(1, &cmdListHandle, nullptr, false); + pCmdq->executeCommandLists(1, &cmdListHandle, nullptr, false, nullptr, 0, nullptr); pCmdq->synchronize(std::numeric_limits::max()); EXPECT_TRUE(csr->expectMemory(outBuffer, &expectedWorkDim, size, AubMemDump::CmdServicesMemTraceMemoryCompare::CompareOperationValues::CompareEqual)); diff --git a/level_zero/core/test/aub_tests/debugger/debugger_aub_tests.cpp b/level_zero/core/test/aub_tests/debugger/debugger_aub_tests.cpp index 3982b79c25..99b4dbfede 100644 --- a/level_zero/core/test/aub_tests/debugger/debugger_aub_tests.cpp +++ b/level_zero/core/test/aub_tests/debugger/debugger_aub_tests.cpp @@ -1,5 +1,5 @@ /* - * Copyright (C) 2021-2023 Intel Corporation + * Copyright (C) 2021-2024 Intel Corporation * * SPDX-License-Identifier: MIT * @@ -130,7 +130,7 @@ HWTEST2_F(DebuggerSingleAddressSpaceAub, GivenSingleAddressSpaceWhenCmdListIsExe EXPECT_EQ(ZE_RESULT_SUCCESS, zeCommandListAppendLaunchKernel(cmdListHandle, kernel, &dispatchTraits, nullptr, 0, nullptr)); commandList->close(); - pCmdq->executeCommandLists(1, &cmdListHandle, nullptr, false); + pCmdq->executeCommandLists(1, &cmdListHandle, nullptr, false, nullptr, 0, nullptr); pCmdq->synchronize(std::numeric_limits::max()); expectMemory(reinterpret_cast(driverHandle->svmAllocsManager->getSVMAlloc(bufferDst)->gpuAllocations.getDefaultGraphicsAllocation()->getGpuAddress()), diff --git a/level_zero/core/test/unit_tests/fixtures/cmdlist_fixture.inl b/level_zero/core/test/unit_tests/fixtures/cmdlist_fixture.inl index e664b66124..0dc8f5be80 100644 --- a/level_zero/core/test/unit_tests/fixtures/cmdlist_fixture.inl +++ b/level_zero/core/test/unit_tests/fixtures/cmdlist_fixture.inl @@ -169,7 +169,7 @@ void CmdListPipelineSelectStateFixture::testBody() { commandList->close(); sizeBefore = cmdQueueStream.getUsed(); - result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); sizeAfter = cmdQueueStream.getUsed(); @@ -255,7 +255,7 @@ void CmdListPipelineSelectStateFixture::testBody() { commandList->close(); sizeBefore = cmdQueueStream.getUsed(); - result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); sizeAfter = cmdQueueStream.getUsed(); @@ -380,7 +380,7 @@ void CmdListPipelineSelectStateFixture::testBody() { commandList->close(); sizeBefore = cmdQueueStream.getUsed(); - result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); sizeAfter = cmdQueueStream.getUsed(); @@ -437,7 +437,7 @@ void CmdListPipelineSelectStateFixture::testBody() { commandList->close(); sizeBefore = cmdQueueStream.getUsed(); - result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); sizeAfter = cmdQueueStream.getUsed(); @@ -509,7 +509,7 @@ void CmdListPipelineSelectStateFixture::testBodyShareStateRegularImmediate() { commandList->close(); sizeBefore = cmdQueueStream.getUsed(); - result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); sizeAfter = cmdQueueStream.getUsed(); @@ -685,7 +685,7 @@ void CmdListPipelineSelectStateFixture::testBodyShareStateImmediateRegular() { commandList->close(); sizeBefore = cmdQueueStream.getUsed(); - result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); sizeAfter = cmdQueueStream.getUsed(); @@ -732,7 +732,7 @@ void CmdListPipelineSelectStateFixture::testBodySystolicAndScratchOnSecondComman // execute first clear command list to settle global init ze_command_list_handle_t commandLists[2] = {commandList->toHandle(), nullptr}; - result = commandQueue->executeCommandLists(1, commandLists, nullptr, true); + result = commandQueue->executeCommandLists(1, commandLists, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); auto queueSize = cmdQueueStream.getUsed(); @@ -740,7 +740,7 @@ void CmdListPipelineSelectStateFixture::testBodySystolicAndScratchOnSecondComman // scratch makes globally front end dirty and so global init too, // but dispatch systolic programming only before second command list commandLists[1] = commandList2->toHandle(); - result = commandQueue->executeCommandLists(2, commandLists, nullptr, true); + result = commandQueue->executeCommandLists(2, commandLists, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); GenCmdList cmdList; @@ -837,7 +837,7 @@ void CmdListThreadArbitrationFixture::testBody() { EXPECT_TRUE(queueCsr->getStateComputeModeDirty()); sizeBefore = cmdQueueStream.getUsed(); - result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); sizeAfter = cmdQueueStream.getUsed(); @@ -906,7 +906,7 @@ void CmdListThreadArbitrationFixture::testBody() { commandList->close(); sizeBefore = cmdQueueStream.getUsed(); - result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); sizeAfter = cmdQueueStream.getUsed(); @@ -996,7 +996,7 @@ void CmdListThreadArbitrationFixture::testBody() { commandList->close(); sizeBefore = cmdQueueStream.getUsed(); - result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); sizeAfter = cmdQueueStream.getUsed(); @@ -1039,7 +1039,7 @@ void CmdListThreadArbitrationFixture::testBody() { commandList->close(); sizeBefore = cmdQueueStream.getUsed(); - result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); sizeAfter = cmdQueueStream.getUsed(); @@ -1104,7 +1104,7 @@ void CmdListLargeGrfFixture::testBody() { EXPECT_TRUE(queueCsr->getStateComputeModeDirty()); sizeBefore = cmdQueueStream.getUsed(); - result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); sizeAfter = cmdQueueStream.getUsed(); @@ -1173,7 +1173,7 @@ void CmdListLargeGrfFixture::testBody() { commandList->close(); sizeBefore = cmdQueueStream.getUsed(); - result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); sizeAfter = cmdQueueStream.getUsed(); @@ -1263,7 +1263,7 @@ void CmdListLargeGrfFixture::testBody() { commandList->close(); sizeBefore = cmdQueueStream.getUsed(); - result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); sizeAfter = cmdQueueStream.getUsed(); @@ -1306,7 +1306,7 @@ void CmdListLargeGrfFixture::testBody() { commandList->close(); sizeBefore = cmdQueueStream.getUsed(); - result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); sizeAfter = cmdQueueStream.getUsed(); diff --git a/level_zero/core/test/unit_tests/gen11/test_cmdqueue_thread_arbitration_policy_gen11.cpp b/level_zero/core/test/unit_tests/gen11/test_cmdqueue_thread_arbitration_policy_gen11.cpp index fd79ace46d..5020515330 100644 --- a/level_zero/core/test/unit_tests/gen11/test_cmdqueue_thread_arbitration_policy_gen11.cpp +++ b/level_zero/core/test/unit_tests/gen11/test_cmdqueue_thread_arbitration_policy_gen11.cpp @@ -1,5 +1,5 @@ /* - * Copyright (C) 2020-2023 Intel Corporation + * Copyright (C) 2020-2024 Intel Corporation * * SPDX-License-Identifier: MIT * @@ -23,7 +23,7 @@ HWTEST2_F(CommandQueueThreadArbitrationPolicyTests, size_t usedSpaceBefore = commandQueue->commandStream.getUsed(); ze_command_list_handle_t hCommandList = commandList->toHandle(); - auto result = commandQueue->executeCommandLists(1, &hCommandList, nullptr, true); + auto result = commandQueue->executeCommandLists(1, &hCommandList, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); size_t usedSpaceAfter = commandQueue->commandStream.getUsed(); @@ -54,7 +54,7 @@ HWTEST2_F(CommandQueueThreadArbitrationPolicyTests, size_t usedSpaceBefore = commandQueue->commandStream.getUsed(); ze_command_list_handle_t hCommandList = commandList->toHandle(); - auto result = commandQueue->executeCommandLists(1, &hCommandList, nullptr, true); + auto result = commandQueue->executeCommandLists(1, &hCommandList, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); size_t usedSpaceAfter = commandQueue->commandStream.getUsed(); @@ -85,7 +85,7 @@ HWTEST2_F(CommandQueueThreadArbitrationPolicyTests, size_t usedSpaceBefore = commandQueue->commandStream.getUsed(); ze_command_list_handle_t hCommandList = commandList->toHandle(); - auto result = commandQueue->executeCommandLists(1, &hCommandList, nullptr, true); + auto result = commandQueue->executeCommandLists(1, &hCommandList, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); size_t usedSpaceAfter = commandQueue->commandStream.getUsed(); diff --git a/level_zero/core/test/unit_tests/gen9/test_cmdqueue_enqueuecommandlist_gen9.cpp b/level_zero/core/test/unit_tests/gen9/test_cmdqueue_enqueuecommandlist_gen9.cpp index 792e763365..bc8eaba91c 100644 --- a/level_zero/core/test/unit_tests/gen9/test_cmdqueue_enqueuecommandlist_gen9.cpp +++ b/level_zero/core/test/unit_tests/gen9/test_cmdqueue_enqueuecommandlist_gen9.cpp @@ -1,5 +1,5 @@ /* - * Copyright (C) 2021-2023 Intel Corporation + * Copyright (C) 2021-2024 Intel Corporation * * SPDX-License-Identifier: MIT * @@ -46,7 +46,7 @@ GEN9TEST_F(CommandQueueExecuteCommandListsGen9, WhenExecutingCmdListsThenPipelin ze_command_list_handle_t commandLists[] = { commandList->toHandle()}; uint32_t numCommandLists = sizeof(commandLists) / sizeof(commandLists[0]); - auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); @@ -89,7 +89,7 @@ GEN9TEST_F(CommandQueueExecuteCommandListsGen9, WhenExecutingCmdListsThenStateBa ze_command_list_handle_t commandLists[] = { commandList->toHandle()}; uint32_t numCommandLists = sizeof(commandLists) / sizeof(commandLists[0]); - auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); @@ -141,7 +141,7 @@ GEN9TEST_F(CommandQueueExecuteCommandListsGen9, WhenExecutingCmdListsThenMidThre ze_command_list_handle_t commandLists[] = {commandList->toHandle()}; uint32_t numCommandLists = sizeof(commandLists) / sizeof(commandLists[0]); - auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); @@ -194,7 +194,7 @@ GEN9TEST_F(CommandQueueExecuteCommandListsGen9, GivenCmdListsWithDifferentPreemp commandListThreadGroup->toHandle(), commandListMidThread->toHandle()}; uint32_t numCommandLists = sizeof(commandLists) / sizeof(commandLists[0]); - auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); diff --git a/level_zero/core/test/unit_tests/gen9/test_cmdqueue_gen9.cpp b/level_zero/core/test/unit_tests/gen9/test_cmdqueue_gen9.cpp index adb35004ff..9d9f8b5b7e 100644 --- a/level_zero/core/test/unit_tests/gen9/test_cmdqueue_gen9.cpp +++ b/level_zero/core/test/unit_tests/gen9/test_cmdqueue_gen9.cpp @@ -1,5 +1,5 @@ /* - * Copyright (C) 2020-2023 Intel Corporation + * Copyright (C) 2020-2024 Intel Corporation * * SPDX-License-Identifier: MIT * @@ -26,7 +26,7 @@ HWTEST2_F(CommandQueueThreadArbitrationPolicyTests, size_t usedSpaceBefore = commandQueue->commandStream.getUsed(); ze_command_list_handle_t hCommandList = commandList->toHandle(); - auto result = commandQueue->executeCommandLists(1, &hCommandList, nullptr, true); + auto result = commandQueue->executeCommandLists(1, &hCommandList, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); size_t usedSpaceAfter = commandQueue->commandStream.getUsed(); @@ -57,7 +57,7 @@ HWTEST2_F(CommandQueueThreadArbitrationPolicyTests, size_t usedSpaceBefore = commandQueue->commandStream.getUsed(); ze_command_list_handle_t hCommandList = commandList->toHandle(); - auto result = commandQueue->executeCommandLists(1, &hCommandList, nullptr, true); + auto result = commandQueue->executeCommandLists(1, &hCommandList, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); size_t usedSpaceAfter = commandQueue->commandStream.getUsed(); @@ -88,7 +88,7 @@ HWTEST2_F(CommandQueueThreadArbitrationPolicyTests, size_t usedSpaceBefore = commandQueue->commandStream.getUsed(); ze_command_list_handle_t hCommandList = commandList->toHandle(); - auto result = commandQueue->executeCommandLists(1, &hCommandList, nullptr, true); + auto result = commandQueue->executeCommandLists(1, &hCommandList, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); size_t usedSpaceAfter = commandQueue->commandStream.getUsed(); diff --git a/level_zero/core/test/unit_tests/mocks/mock_cmdqueue.h b/level_zero/core/test/unit_tests/mocks/mock_cmdqueue.h index 1c9a2d2551..b2dfa044ae 100644 --- a/level_zero/core/test/unit_tests/mocks/mock_cmdqueue.h +++ b/level_zero/core/test/unit_tests/mocks/mock_cmdqueue.h @@ -1,5 +1,5 @@ /* - * Copyright (C) 2020-2023 Intel Corporation + * Copyright (C) 2020-2024 Intel Corporation * * SPDX-License-Identifier: MIT * @@ -60,7 +60,7 @@ struct Mock : public CommandQueue { ADDMETHOD_NOBASE(createFence, ze_result_t, ZE_RESULT_SUCCESS, (const ze_fence_desc_t *desc, ze_fence_handle_t *phFence)); ADDMETHOD_NOBASE(destroy, ze_result_t, ZE_RESULT_SUCCESS, ()); - ADDMETHOD_NOBASE(executeCommandLists, ze_result_t, ZE_RESULT_SUCCESS, (uint32_t numCommandLists, ze_command_list_handle_t *phCommandLists, ze_fence_handle_t hFence, bool performMigration)); + ADDMETHOD_NOBASE(executeCommandLists, ze_result_t, ZE_RESULT_SUCCESS, (uint32_t numCommandLists, ze_command_list_handle_t *phCommandLists, ze_fence_handle_t hFence, bool performMigration, ze_event_handle_t hSignalEvent, uint32_t numWaitEvents, ze_event_handle_t *phWaitEvents)); ADDMETHOD_NOBASE(executeCommands, ze_result_t, ZE_RESULT_SUCCESS, (uint32_t numCommands, void *phCommands, ze_fence_handle_t hFence)); ADDMETHOD_NOBASE(synchronize, ze_result_t, ZE_RESULT_SUCCESS, (uint64_t timeout)); ADDMETHOD_NOBASE(getPreemptionCmdProgramming, bool, false, ()); diff --git a/level_zero/core/test/unit_tests/os_interface/linux/cmdqueue_linux_tests.cpp b/level_zero/core/test/unit_tests/os_interface/linux/cmdqueue_linux_tests.cpp index 042134a6b0..62e5437b6d 100644 --- a/level_zero/core/test/unit_tests/os_interface/linux/cmdqueue_linux_tests.cpp +++ b/level_zero/core/test/unit_tests/os_interface/linux/cmdqueue_linux_tests.cpp @@ -1,5 +1,5 @@ /* - * Copyright (C) 2022-2023 Intel Corporation + * Copyright (C) 2022-2024 Intel Corporation * * SPDX-License-Identifier: MIT * @@ -69,7 +69,7 @@ HWTEST2_F(CommandQueueLinuxTests, givenExecBufferErrorOnXeHpcWhenExecutingComman ze_command_list_handle_t cmdListHandles[1] = {commandList->toHandle()}; - returnValue = commandQueue->executeCommandLists(1, cmdListHandles, nullptr, false); + returnValue = commandQueue->executeCommandLists(1, cmdListHandles, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_ERROR_OUT_OF_HOST_MEMORY, returnValue); commandQueue->destroy(); neoDevice->getMemoryManager()->freeGraphicsMemory(kernel.immutableData.isaGraphicsAllocation.release()); diff --git a/level_zero/core/test/unit_tests/sources/assert/test_assert.cpp b/level_zero/core/test/unit_tests/sources/assert/test_assert.cpp index 1b1dafbf2e..20a2f61102 100644 --- a/level_zero/core/test/unit_tests/sources/assert/test_assert.cpp +++ b/level_zero/core/test/unit_tests/sources/assert/test_assert.cpp @@ -1,5 +1,5 @@ /* - * Copyright (C) 2020-2023 Intel Corporation + * Copyright (C) 2020-2024 Intel Corporation * * SPDX-License-Identifier: MIT * @@ -370,7 +370,7 @@ TEST_F(CommandQueueWithAssert, GivenCmdListWithAssertWhenExecutingThenCommandQue commandList->close(); ze_command_list_handle_t cmdListHandle = commandList->toHandle(); - returnValue = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, false); + returnValue = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, returnValue); EXPECT_TRUE(commandQueue->cmdListWithAssertExecuted); diff --git a/level_zero/core/test/unit_tests/sources/cmdlist/test_cmdlist_2.cpp b/level_zero/core/test/unit_tests/sources/cmdlist/test_cmdlist_2.cpp index 3ea9e77b4d..41b629282b 100644 --- a/level_zero/core/test/unit_tests/sources/cmdlist/test_cmdlist_2.cpp +++ b/level_zero/core/test/unit_tests/sources/cmdlist/test_cmdlist_2.cpp @@ -1,5 +1,5 @@ /* - * Copyright (C) 2020-2023 Intel Corporation + * Copyright (C) 2020-2024 Intel Corporation * * SPDX-License-Identifier: MIT * @@ -1546,7 +1546,7 @@ HWTEST_F(PrimaryBatchBufferCmdListTest, givenRegularCmdListWhenFlushingThenPassS EXPECT_EQ(ZE_RESULT_SUCCESS, commandList->close()); auto cmdListHandle = commandList->toHandle(); - EXPECT_EQ(ZE_RESULT_SUCCESS, commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true)); + EXPECT_EQ(ZE_RESULT_SUCCESS, commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr)); EXPECT_TRUE(ultCsr->latestFlushedBatchBuffer.hasStallingCmds); } @@ -1563,7 +1563,7 @@ HWTEST_F(PrimaryBatchBufferCmdListTest, givenCmdListWhenCallingSynchronizeThenUn auto numClients = csr->getNumClients(); auto cmdListHandle = commandList->toHandle(); - EXPECT_EQ(ZE_RESULT_SUCCESS, commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true)); + EXPECT_EQ(ZE_RESULT_SUCCESS, commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr)); EXPECT_EQ(numClients + 1, csr->getNumClients()); @@ -1647,7 +1647,7 @@ HWTEST_F(PrimaryBatchBufferCmdListTest, givenPrimaryBatchBufferWhenCopyCommandLi size_t blitterContextInitSize = ultCsr->getCmdsSizeForHardwareContext(); auto cmdListHandle = commandListCopy->toHandle(); - returnValue = commandQueueCopy->executeCommandLists(1, &cmdListHandle, nullptr, true); + returnValue = commandQueueCopy->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, returnValue); auto bbStartCmd = genCmdCast(bbStartSpace); @@ -1662,7 +1662,7 @@ HWTEST_F(PrimaryBatchBufferCmdListTest, givenPrimaryBatchBufferWhenCopyCommandLi } size_t queueSizeUsed = cmdQueueStream.getUsed(); - returnValue = commandQueueCopy->executeCommandLists(1, &cmdListHandle, nullptr, true); + returnValue = commandQueueCopy->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, returnValue); bbStartCmd = genCmdCast(bbStartSpace); @@ -1715,7 +1715,7 @@ HWTEST2_F(PrimaryBatchBufferPreamblelessCmdListTest, // first command list settles global init and leaves state as uncached MOCS auto commandListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); auto &cmdQueueStream = commandQueue->commandStream; @@ -1724,7 +1724,7 @@ HWTEST2_F(PrimaryBatchBufferPreamblelessCmdListTest, ze_command_list_handle_t sameCommandListTwice[] = {commandList2->toHandle(), commandList2->toHandle()}; // second command list requires uncached MOCS state, so no dynamic preamble for the fist instance, but leaves cached MOCS state // second instance require dynamic preamble to reload MOCS to uncached state - result = commandQueue->executeCommandLists(2, sameCommandListTwice, nullptr, true); + result = commandQueue->executeCommandLists(2, sameCommandListTwice, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); GenCmdList cmdList; @@ -1758,7 +1758,7 @@ HWTEST2_F(PrimaryBatchBufferPreamblelessCmdListTest, EXPECT_EQ(ZE_RESULT_SUCCESS, result); auto commandListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); auto &cmdQueueStream = commandQueue->commandStream; @@ -1767,7 +1767,7 @@ HWTEST2_F(PrimaryBatchBufferPreamblelessCmdListTest, size_t queueUsedSize = cmdQueueStream.getUsed(); auto gpuReturnAddress = cmdQueueStream.getGpuBase() + queueUsedSize; - result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); auto &cmdContainer = commandList->getCmdContainer(); @@ -1800,7 +1800,7 @@ HWTEST2_F(PrimaryBatchBufferPreamblelessCmdListTest, commandList2->toHandle(), commandList3->toHandle()}; - result = commandQueue->executeCommandLists(1, commandLists, nullptr, true); + result = commandQueue->executeCommandLists(1, commandLists, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); auto &cmdQueueStream = commandQueue->commandStream; @@ -1821,7 +1821,7 @@ HWTEST2_F(PrimaryBatchBufferPreamblelessCmdListTest, result = commandList3->close(); EXPECT_EQ(ZE_RESULT_SUCCESS, result); - result = commandQueue->executeCommandLists(3, commandLists, nullptr, true); + result = commandQueue->executeCommandLists(3, commandLists, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); GenCmdList cmdList; @@ -1876,7 +1876,7 @@ HWTEST2_F(PrimaryBatchBufferPreamblelessCmdListTest, commandList2->toHandle(), commandList3->toHandle()}; - result = commandQueue->executeCommandLists(1, commandLists, nullptr, true); + result = commandQueue->executeCommandLists(1, commandLists, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); auto &cmdQueueStream = commandQueue->commandStream; @@ -1899,7 +1899,7 @@ HWTEST2_F(PrimaryBatchBufferPreamblelessCmdListTest, result = commandList3->close(); EXPECT_EQ(ZE_RESULT_SUCCESS, result); - result = commandQueue->executeCommandLists(3, commandLists, nullptr, true); + result = commandQueue->executeCommandLists(3, commandLists, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); // 1st command list is preambleless diff --git a/level_zero/core/test/unit_tests/sources/cmdlist/test_cmdlist_3.cpp b/level_zero/core/test/unit_tests/sources/cmdlist/test_cmdlist_3.cpp index 7681dbf74c..7b3866216b 100644 --- a/level_zero/core/test/unit_tests/sources/cmdlist/test_cmdlist_3.cpp +++ b/level_zero/core/test/unit_tests/sources/cmdlist/test_cmdlist_3.cpp @@ -1637,7 +1637,7 @@ HWTEST2_F(FrontEndPrimaryBatchBufferCommandListTest, EXPECT_EQ(ZE_RESULT_SUCCESS, result); auto commandListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); if (fePropertiesSupport.disableEuFusion) { @@ -1748,7 +1748,7 @@ HWTEST2_F(FrontEndPrimaryBatchBufferCommandListTest, EXPECT_EQ(ZE_RESULT_SUCCESS, result); auto commandListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); if (fePropertiesSupport.computeDispatchAllWalker) { diff --git a/level_zero/core/test/unit_tests/sources/cmdlist/test_cmdlist_5.cpp b/level_zero/core/test/unit_tests/sources/cmdlist/test_cmdlist_5.cpp index c3e2867248..4a88175793 100644 --- a/level_zero/core/test/unit_tests/sources/cmdlist/test_cmdlist_5.cpp +++ b/level_zero/core/test/unit_tests/sources/cmdlist/test_cmdlist_5.cpp @@ -1179,7 +1179,7 @@ HWTEST2_F(CommandListStateBaseAddressPrivateHeapTest, size_t queueBefore = cmdQueueStream.getUsed(); ze_command_list_handle_t cmdListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); size_t queueAfter = cmdQueueStream.getUsed(); @@ -1229,7 +1229,7 @@ HWTEST2_F(CommandListStateBaseAddressPrivateHeapTest, queueBefore = cmdQueueStream.getUsed(); cmdListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); queueAfter = cmdQueueStream.getUsed(); @@ -1375,7 +1375,7 @@ HWTEST2_F(CommandListStateBaseAddressPrivateHeapTest, size_t queueBefore = cmdQueueStream.getUsed(); ze_command_list_handle_t cmdListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); size_t queueAfter = cmdQueueStream.getUsed(); @@ -1415,7 +1415,7 @@ HWTEST2_F(CommandListStateBaseAddressPrivateHeapTest, queueBefore = cmdQueueStream.getUsed(); cmdListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); queueAfter = cmdQueueStream.getUsed(); @@ -1556,7 +1556,7 @@ HWTEST2_F(CommandListBindlessSshPrivateHeapTest, size_t queueBefore = cmdQueueStream.getUsed(); ze_command_list_handle_t cmdListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); size_t queueAfter = cmdQueueStream.getUsed(); @@ -1588,7 +1588,7 @@ HWTEST2_F(CommandListBindlessSshPrivateHeapTest, queueBefore = cmdQueueStream.getUsed(); cmdListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); queueAfter = cmdQueueStream.getUsed(); @@ -1640,7 +1640,7 @@ HWTEST2_F(CommandListBindlessSshPrivateHeapTest, size_t queueBefore = cmdQueueStream.getUsed(); ze_command_list_handle_t cmdListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); size_t queueAfter = cmdQueueStream.getUsed(); @@ -1719,7 +1719,7 @@ HWTEST2_F(CommandListBindlessSshPrivateHeapTest, auto &cmdQueueStream = commandQueue->commandStream; size_t queueBefore = cmdQueueStream.getUsed(); ze_command_list_handle_t cmdListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); size_t queueAfter = cmdQueueStream.getUsed(); @@ -1799,7 +1799,7 @@ HWTEST2_F(CommandListBindlessSshPrivateHeapTest, auto &cmdQueueStream = commandQueue->commandStream; size_t queueBefore = cmdQueueStream.getUsed(); ze_command_list_handle_t cmdListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); size_t queueAfter = cmdQueueStream.getUsed(); @@ -2188,7 +2188,7 @@ HWTEST2_F(CommandListStateBaseAddressPrivateHeapTest, size_t queueBefore = cmdQueueStream.getUsed(); ze_command_list_handle_t cmdListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); size_t queueAfter = cmdQueueStream.getUsed(); @@ -2462,7 +2462,7 @@ HWTEST2_F(CommandListStateBaseAddressPrivateHeapTest, size_t queueBefore = cmdQueueStream.getUsed(); ze_command_list_handle_t cmdListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); size_t queueAfter = cmdQueueStream.getUsed(); @@ -2552,7 +2552,7 @@ HWTEST2_F(CommandListStateBaseAddressPrivateHeapTest, size_t queueBefore = cmdQueueStream.getUsed(); ze_command_list_handle_t cmdListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); size_t queueAfter = cmdQueueStream.getUsed(); @@ -2621,7 +2621,7 @@ HWTEST2_F(CommandListStateBaseAddressPrivateHeapTest, size_t queueBefore = cmdQueueStream.getUsed(); ze_command_list_handle_t cmdListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); size_t queueAfter = cmdQueueStream.getUsed(); @@ -2719,7 +2719,7 @@ HWTEST2_F(CommandListStateBaseAddressPrivateHeapTest, size_t queueBefore = cmdQueueStream.getUsed(); ze_command_list_handle_t cmdListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); size_t queueAfter = cmdQueueStream.getUsed(); @@ -2793,7 +2793,7 @@ HWTEST2_F(CommandListStateBaseAddressPrivateHeapTest, size_t queueBefore = cmdQueueStream.getUsed(); ze_command_list_handle_t cmdListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); size_t queueAfter = cmdQueueStream.getUsed(); @@ -2947,7 +2947,7 @@ HWTEST2_F(CommandListStateBaseAddressPrivateHeapTest, size_t queueBefore = cmdQueueStream.getUsed(); ze_command_list_handle_t cmdListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); size_t queueAfter = cmdQueueStream.getUsed(); @@ -2978,7 +2978,7 @@ HWTEST2_F(CommandListStateBaseAddressPrivateHeapTest, EXPECT_NE(firstHeapSurfaceBaseAddress, secondHeapSurfaceBaseAddress); queueBefore = cmdQueueStream.getUsed(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); queueAfter = cmdQueueStream.getUsed(); @@ -3017,7 +3017,7 @@ HWTEST2_F(CommandListStateBaseAddressPrivateHeapTest, size_t queueBefore = cmdQueueStream.getUsed(); ze_command_list_handle_t cmdListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); size_t queueAfter = cmdQueueStream.getUsed(); @@ -3067,7 +3067,7 @@ HWTEST2_F(CommandListStateBaseAddressPrivateHeapTest, EXPECT_EQ(secondHeapSurfaceBaseAddress, sbaCmd->getSurfaceStateBaseAddress()); queueBefore = cmdQueueStream.getUsed(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); queueAfter = cmdQueueStream.getUsed(); @@ -3097,7 +3097,7 @@ HWTEST2_F(CommandListStateBaseAddressPrivateHeapTest, EXPECT_EQ(ZE_RESULT_SUCCESS, returnValue); auto cmdListHandle = cmdListObject->toHandle(); - returnValue = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + returnValue = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, returnValue); returnValue = cmdListObject->destroy(); diff --git a/level_zero/core/test/unit_tests/sources/cmdlist/test_cmdlist_6.cpp b/level_zero/core/test/unit_tests/sources/cmdlist/test_cmdlist_6.cpp index d3216a9910..2f27b74e6b 100644 --- a/level_zero/core/test/unit_tests/sources/cmdlist/test_cmdlist_6.cpp +++ b/level_zero/core/test/unit_tests/sources/cmdlist/test_cmdlist_6.cpp @@ -1321,7 +1321,7 @@ HWTEST2_F(CommandListStateBaseAddressGlobalStatelessTest, givenGlobalStatelessWh commandList->close(); ze_command_list_handle_t cmdListHandle = commandList->toHandle(); - auto result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + auto result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); EXPECT_TRUE(ultCsr->isMadeResident(globalStatelessAlloc)); @@ -1381,7 +1381,7 @@ HWTEST2_F(CommandListStateBaseAddressGlobalStatelessTest, size_t queueBefore = cmdQueueStream.getUsed(); ze_command_list_handle_t cmdListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); size_t queueAfter = cmdQueueStream.getUsed(); @@ -1524,7 +1524,7 @@ HWTEST2_F(CommandListStateBaseAddressGlobalStatelessTest, size_t queueBefore = cmdQueueStream.getUsed(); ze_command_list_handle_t cmdListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); size_t queueAfter = cmdQueueStream.getUsed(); @@ -1636,7 +1636,7 @@ HWTEST2_F(CommandListStateBaseAddressGlobalStatelessTest, size_t queueBefore = cmdQueueStream.getUsed(); ze_command_list_handle_t cmdListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); size_t queueAfter = cmdQueueStream.getUsed(); @@ -1703,7 +1703,7 @@ HWTEST2_F(CommandListStateBaseAddressGlobalStatelessTest, size_t queueBefore = cmdQueueStream.getUsed(); ze_command_list_handle_t cmdListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); size_t queueAfter = cmdQueueStream.getUsed(); @@ -1813,7 +1813,7 @@ HWTEST2_F(CommandListStateBaseAddressGlobalStatelessTest, queueBefore = cmdQueueStream.getUsed(); cmdListHandle = commandListPrivateHeap->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); queueAfter = cmdQueueStream.getUsed(); @@ -1944,7 +1944,7 @@ HWTEST2_F(CommandListStateBaseAddressGlobalStatelessTest, size_t queueBefore = cmdQueueStream.getUsed(); ze_command_list_handle_t cmdListHandle = commandListPrivateHeap->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); size_t queueAfter = cmdQueueStream.getUsed(); @@ -2039,7 +2039,7 @@ HWTEST2_F(CommandListStateBaseAddressGlobalStatelessTest, queueBefore = cmdQueueStream.getUsed(); cmdListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); queueAfter = cmdQueueStream.getUsed(); @@ -2227,7 +2227,7 @@ HWTEST2_F(CommandListStateBaseAddressGlobalStatelessTest, size_t queueBefore = cmdQueueStream.getUsed(); ze_command_list_handle_t cmdListHandle = commandListPrivateHeap->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); size_t queueAfter = cmdQueueStream.getUsed(); @@ -2358,7 +2358,7 @@ HWTEST2_F(CommandListStateBaseAddressGlobalStatelessTest, size_t queueBefore = cmdQueueStream.getUsed(); ze_command_list_handle_t cmdListHandle = commandListPrivateHeap->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); size_t queueAfter = cmdQueueStream.getUsed(); @@ -2492,7 +2492,7 @@ HWTEST2_F(CommandListStateBaseAddressGlobalStatelessTest, size_t queueBefore = cmdQueueStream.getUsed(); ze_command_list_handle_t cmdListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); size_t queueAfter = cmdQueueStream.getUsed(); @@ -2603,7 +2603,7 @@ HWTEST2_F(CommandListStateBaseAddressGlobalStatelessTest, EXPECT_EQ(ZE_RESULT_SUCCESS, returnValue); auto cmdListHandle = cmdListObject->toHandle(); - returnValue = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + returnValue = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, returnValue); returnValue = cmdListObject->destroy(); diff --git a/level_zero/core/test/unit_tests/sources/cmdlist/test_cmdlist_7.cpp b/level_zero/core/test/unit_tests/sources/cmdlist/test_cmdlist_7.cpp index 65f96339fa..c705b9eedf 100644 --- a/level_zero/core/test/unit_tests/sources/cmdlist/test_cmdlist_7.cpp +++ b/level_zero/core/test/unit_tests/sources/cmdlist/test_cmdlist_7.cpp @@ -1185,7 +1185,7 @@ HWTEST2_F(FrontEndMultiReturnCommandListTest, size_t usedBefore = cmdQueueStream.getUsed(); auto cmdListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, false); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); size_t usedAfter = cmdQueueStream.getUsed(); @@ -1434,7 +1434,7 @@ HWTEST2_F(FrontEndMultiReturnCommandListTest, size_t usedBefore = cmdQueueStream.getUsed(); auto cmdListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, false); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); size_t usedAfter = cmdQueueStream.getUsed(); @@ -1673,7 +1673,7 @@ HWTEST2_F(FrontEndMultiReturnCommandListTest, givenCmdQueueAndImmediateCmdListUs auto cmdListHandle = commandList->toHandle(); usedBefore = cmdQueueStream.getUsed(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, false); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); usedAfter = cmdQueueStream.getUsed(); @@ -1852,7 +1852,7 @@ HWTEST2_F(FrontEndMultiReturnCommandListTest, givenCmdQueueAndImmediateCmdListUs auto cmdListHandle = commandList->toHandle(); usedBefore = cmdQueueStream.getUsed(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, false); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); usedAfter = cmdQueueStream.getUsed(); diff --git a/level_zero/core/test/unit_tests/sources/cmdlist/test_cmdlist_append_launch_kernel_1.cpp b/level_zero/core/test/unit_tests/sources/cmdlist/test_cmdlist_append_launch_kernel_1.cpp index 4f7cf0ae6c..cc4e84a053 100644 --- a/level_zero/core/test/unit_tests/sources/cmdlist/test_cmdlist_append_launch_kernel_1.cpp +++ b/level_zero/core/test/unit_tests/sources/cmdlist/test_cmdlist_append_launch_kernel_1.cpp @@ -403,7 +403,7 @@ HWTEST_F(CommandListAppendLaunchKernel, givenKernelWithPrintfAppendedToCommandLi auto commandListHandle = commandList->toHandle(); EXPECT_EQ(0u, kernel->printPrintfOutputCalledTimes); - EXPECT_EQ(ZE_RESULT_SUCCESS, commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false)); + EXPECT_EQ(ZE_RESULT_SUCCESS, commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr)); EXPECT_EQ(ZE_RESULT_SUCCESS, commandQueue->synchronize(std::numeric_limits::max())); EXPECT_EQ(1u, kernel->printPrintfOutputCalledTimes); EXPECT_EQ(ZE_RESULT_SUCCESS, kernel->destroy()); @@ -465,7 +465,7 @@ HWTEST_F(CommandListAppendLaunchKernel, givenKernelWithPrintfAndEventAppendedToC auto commandListHandle = commandList->toHandle(); EXPECT_EQ(0u, kernel->printPrintfOutputCalledTimes); - EXPECT_EQ(ZE_RESULT_SUCCESS, commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false)); + EXPECT_EQ(ZE_RESULT_SUCCESS, commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr)); EXPECT_EQ(ZE_RESULT_SUCCESS, commandQueue->synchronize(std::numeric_limits::max())); *reinterpret_cast(event->getHostAddress()) = Event::STATE_SIGNALED; EXPECT_EQ(1u, kernel->printPrintfOutputCalledTimes); @@ -532,7 +532,7 @@ HWTEST_F(CommandListAppendLaunchKernel, givenKernelWithPrintfAndEventAppendedToC auto commandListHandle = commandList->toHandle(); EXPECT_EQ(0u, kernel->printPrintfOutputCalledTimes); - EXPECT_EQ(ZE_RESULT_SUCCESS, commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false)); + EXPECT_EQ(ZE_RESULT_SUCCESS, commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr)); *reinterpret_cast(event->getHostAddress()) = Event::STATE_SIGNALED; EXPECT_EQ(ZE_RESULT_SUCCESS, event->hostSynchronize(std::numeric_limits::max())); EXPECT_EQ(1u, kernel->printPrintfOutputCalledTimes); diff --git a/level_zero/core/test/unit_tests/sources/cmdlist/test_cmdlist_xehp_and_later.cpp b/level_zero/core/test/unit_tests/sources/cmdlist/test_cmdlist_xehp_and_later.cpp index 34ba0a0b86..27bf4094e4 100644 --- a/level_zero/core/test/unit_tests/sources/cmdlist/test_cmdlist_xehp_and_later.cpp +++ b/level_zero/core/test/unit_tests/sources/cmdlist/test_cmdlist_xehp_and_later.cpp @@ -1694,7 +1694,7 @@ HWTEST2_F(RayTracingCmdListTest, size_t queueSizeBefore = cmdQueueStream.getUsed(); ze_command_list_handle_t cmdListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); size_t queueSizeAfter = cmdQueueStream.getUsed(); @@ -1705,7 +1705,7 @@ HWTEST2_F(RayTracingCmdListTest, ultCsr->isMadeResident(rtAllocation, residentCount); queueSizeBefore = cmdQueueStream.getUsed(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); queueSizeAfter = cmdQueueStream.getUsed(); @@ -1744,7 +1744,7 @@ HWTEST2_F(RayTracingCmdListTest, size_t queueSizeBefore = cmdQueueStream.getUsed(); ze_command_list_handle_t cmdListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); size_t queueSizeAfter = cmdQueueStream.getUsed(); @@ -1865,7 +1865,7 @@ HWTEST2_F(RayTracingCmdListTest, size_t queueSizeBefore = cmdQueueStream.getUsed(); ze_command_list_handle_t cmdListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); size_t queueSizeAfter = cmdQueueStream.getUsed(); @@ -2265,7 +2265,7 @@ HWTEST2_F(ImmediateFlushTaskCsrSharedHeapCmdListTest, } ze_command_list_handle_t cmdListHandle = commandList->toHandle(); - result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); auto &csrBaseAddressState = csrImmediate.getStreamProperties().stateBaseAddress; diff --git a/level_zero/core/test/unit_tests/sources/cmdlist/test_in_order_cmdlist.cpp b/level_zero/core/test/unit_tests/sources/cmdlist/test_in_order_cmdlist.cpp index 88ea46d1e7..b4101c25c3 100644 --- a/level_zero/core/test/unit_tests/sources/cmdlist/test_in_order_cmdlist.cpp +++ b/level_zero/core/test/unit_tests/sources/cmdlist/test_in_order_cmdlist.cpp @@ -2488,19 +2488,19 @@ HWTEST2_F(InOrderCmdListTests, givenEventGeneratedByRegularCmdListWhenWaitingFro // 1 Execute call offset = cmdStream->getUsed(); - mockCmdQHw->executeCommandLists(1, ®ularCmdListHandle, nullptr, false); + mockCmdQHw->executeCommandLists(1, ®ularCmdListHandle, nullptr, false, nullptr, 0, nullptr); immCmdList->appendLaunchKernel(kernel->toHandle(), groupCount, nullptr, 1, &eventHandle, launchParams, false); verifySemaphore(expectedCounterValue); // 2 Execute calls offset = cmdStream->getUsed(); - mockCmdQHw->executeCommandLists(1, ®ularCmdListHandle, nullptr, false); + mockCmdQHw->executeCommandLists(1, ®ularCmdListHandle, nullptr, false, nullptr, 0, nullptr); immCmdList->appendLaunchKernel(kernel->toHandle(), groupCount, nullptr, 1, &eventHandle, launchParams, false); verifySemaphore(expectedCounterValue + expectedCounterAppendValue); // 3 Execute calls offset = cmdStream->getUsed(); - mockCmdQHw->executeCommandLists(1, ®ularCmdListHandle, nullptr, false); + mockCmdQHw->executeCommandLists(1, ®ularCmdListHandle, nullptr, false, nullptr, 0, nullptr); immCmdList->appendLaunchKernel(kernel->toHandle(), groupCount, nullptr, 1, &eventHandle, launchParams, false); verifySemaphore(expectedCounterValue + (expectedCounterAppendValue * 2)); } @@ -3637,8 +3637,8 @@ HWTEST2_F(InOrderCmdListTests, givenCounterBasedEventWhenAskingForEventAddressAn mockCmdQHw->initialize(false, false, false); auto cmdListHandle = cmdList->toHandle(); - mockCmdQHw->executeCommandLists(1, &cmdListHandle, nullptr, false); - mockCmdQHw->executeCommandLists(1, &cmdListHandle, nullptr, false); + mockCmdQHw->executeCommandLists(1, &cmdListHandle, nullptr, false, nullptr, 0, nullptr); + mockCmdQHw->executeCommandLists(1, &cmdListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, zexEventGetDeviceAddress(eventHandle, &counterValue, &address)); EXPECT_EQ(4u, counterValue); @@ -4327,13 +4327,13 @@ HWTEST2_F(MultiTileInOrderCmdListTests, whenUsingRegularCmdListThenAddWalkerToPa auto handle = regularCmdList->toHandle(); - mockCmdQHw->executeCommandLists(1, &handle, nullptr, false); + mockCmdQHw->executeCommandLists(1, &handle, nullptr, false, nullptr, 0, nullptr); verifyPatching(0); - mockCmdQHw->executeCommandLists(1, &handle, nullptr, false); + mockCmdQHw->executeCommandLists(1, &handle, nullptr, false, nullptr, 0, nullptr); verifyPatching(1); - mockCmdQHw->executeCommandLists(1, &handle, nullptr, false); + mockCmdQHw->executeCommandLists(1, &handle, nullptr, false, nullptr, 0, nullptr); verifyPatching(2); } @@ -4813,18 +4813,18 @@ HWTEST2_F(InOrderRegularCmdListTests, whenUsingRegularCmdListThenAddCmdsToPatch, auto handle = regularCmdList->toHandle(); - mockCmdQHw->executeCommandLists(1, &handle, nullptr, false); + mockCmdQHw->executeCommandLists(1, &handle, nullptr, false, nullptr, 0, nullptr); verifyPatching(0); - mockCmdQHw->executeCommandLists(1, &handle, nullptr, false); + mockCmdQHw->executeCommandLists(1, &handle, nullptr, false, nullptr, 0, nullptr); verifyPatching(1); - mockCmdQHw->executeCommandLists(1, &handle, nullptr, false); + mockCmdQHw->executeCommandLists(1, &handle, nullptr, false, nullptr, 0, nullptr); verifyPatching(2); if (regularCmdList->isQwordInOrderCounter()) { regularCmdList->inOrderExecInfo->addRegularCmdListSubmissionCounter(static_cast(std::numeric_limits::max()) + 3); - mockCmdQHw->executeCommandLists(1, &handle, nullptr, false); + mockCmdQHw->executeCommandLists(1, &handle, nullptr, false, nullptr, 0, nullptr); verifyPatching(regularCmdList->inOrderExecInfo->getRegularCmdListSubmissionCounter() - 1); } @@ -4884,14 +4884,14 @@ HWTEST2_F(InOrderRegularCmdListTests, givenCrossRegularCmdListDependenciesWhenEx auto cmdListHandle1 = regularCmdList1->toHandle(); auto cmdListHandle2 = regularCmdList2->toHandle(); - mockCmdQHw->executeCommandLists(1, &cmdListHandle2, nullptr, false); - mockCmdQHw->executeCommandLists(1, &cmdListHandle2, nullptr, false); - mockCmdQHw->executeCommandLists(1, &cmdListHandle2, nullptr, false); + mockCmdQHw->executeCommandLists(1, &cmdListHandle2, nullptr, false, nullptr, 0, nullptr); + mockCmdQHw->executeCommandLists(1, &cmdListHandle2, nullptr, false, nullptr, 0, nullptr); + mockCmdQHw->executeCommandLists(1, &cmdListHandle2, nullptr, false, nullptr, 0, nullptr); verifyPatching(5, baseEventWaitValue); - mockCmdQHw->executeCommandLists(1, &cmdListHandle1, nullptr, false); - mockCmdQHw->executeCommandLists(1, &cmdListHandle2, nullptr, false); + mockCmdQHw->executeCommandLists(1, &cmdListHandle1, nullptr, false, nullptr, 0, nullptr); + mockCmdQHw->executeCommandLists(1, &cmdListHandle2, nullptr, false, nullptr, 0, nullptr); verifyPatching(7, baseEventWaitValue); } @@ -4925,9 +4925,9 @@ HWTEST2_F(InOrderRegularCmdListTests, givenCrossRegularCmdListDependenciesWhenEx auto cmdListHandle1 = regularCmdList1->toHandle(); auto cmdListHandle2 = regularCmdList2->toHandle(); - mockCmdQHw->executeCommandLists(1, &cmdListHandle1, nullptr, false); - mockCmdQHw->executeCommandLists(1, &cmdListHandle1, nullptr, false); - mockCmdQHw->executeCommandLists(1, &cmdListHandle1, nullptr, false); + mockCmdQHw->executeCommandLists(1, &cmdListHandle1, nullptr, false, nullptr, 0, nullptr); + mockCmdQHw->executeCommandLists(1, &cmdListHandle1, nullptr, false, nullptr, 0, nullptr); + mockCmdQHw->executeCommandLists(1, &cmdListHandle1, nullptr, false, nullptr, 0, nullptr); auto cmdStream2 = regularCmdList2->getCmdContainer().getCommandStream(); @@ -4959,17 +4959,17 @@ HWTEST2_F(InOrderRegularCmdListTests, givenCrossRegularCmdListDependenciesWhenEx verifyPatching(1, baseEventWaitValue); - mockCmdQHw->executeCommandLists(1, &cmdListHandle2, nullptr, false); + mockCmdQHw->executeCommandLists(1, &cmdListHandle2, nullptr, false, nullptr, 0, nullptr); verifyPatching(1, baseEventWaitValue + (2 * regularCmdList1->inOrderExecInfo->getCounterValue())); - mockCmdQHw->executeCommandLists(1, &cmdListHandle2, nullptr, false); - mockCmdQHw->executeCommandLists(1, &cmdListHandle2, nullptr, false); + mockCmdQHw->executeCommandLists(1, &cmdListHandle2, nullptr, false, nullptr, 0, nullptr); + mockCmdQHw->executeCommandLists(1, &cmdListHandle2, nullptr, false, nullptr, 0, nullptr); verifyPatching(5, baseEventWaitValue + (2 * regularCmdList1->inOrderExecInfo->getCounterValue())); - mockCmdQHw->executeCommandLists(1, &cmdListHandle1, nullptr, false); - mockCmdQHw->executeCommandLists(1, &cmdListHandle2, nullptr, false); + mockCmdQHw->executeCommandLists(1, &cmdListHandle1, nullptr, false, nullptr, 0, nullptr); + mockCmdQHw->executeCommandLists(1, &cmdListHandle2, nullptr, false, nullptr, 0, nullptr); verifyPatching(7, baseEventWaitValue + (3 * regularCmdList1->inOrderExecInfo->getCounterValue())); } @@ -5048,13 +5048,13 @@ HWTEST2_F(InOrderRegularCmdListTests, whenUsingRegularCmdListThenAddWalkerToPatc auto handle = regularCmdList->toHandle(); - mockCmdQHw->executeCommandLists(1, &handle, nullptr, false); + mockCmdQHw->executeCommandLists(1, &handle, nullptr, false, nullptr, 0, nullptr); verifyPatching(0); - mockCmdQHw->executeCommandLists(1, &handle, nullptr, false); + mockCmdQHw->executeCommandLists(1, &handle, nullptr, false, nullptr, 0, nullptr); verifyPatching(1); - mockCmdQHw->executeCommandLists(1, &handle, nullptr, false); + mockCmdQHw->executeCommandLists(1, &handle, nullptr, false, nullptr, 0, nullptr); verifyPatching(2); } @@ -5357,19 +5357,19 @@ HWTEST2_F(InOrderRegularCmdListTests, givenNonInOrderRegularCmdListWhenPassingCo auto inOrderRegularCmdListHandle = inOrderRegularCmdList->toHandle(); auto regularHandle = regularCmdList->toHandle(); - mockCmdQHw->executeCommandLists(1, &inOrderRegularCmdListHandle, nullptr, false); - mockCmdQHw->executeCommandLists(1, ®ularHandle, nullptr, false); + mockCmdQHw->executeCommandLists(1, &inOrderRegularCmdListHandle, nullptr, false, nullptr, 0, nullptr); + mockCmdQHw->executeCommandLists(1, ®ularHandle, nullptr, false, nullptr, 0, nullptr); verifyPatching(0); - mockCmdQHw->executeCommandLists(1, &inOrderRegularCmdListHandle, nullptr, false); - mockCmdQHw->executeCommandLists(1, ®ularHandle, nullptr, false); + mockCmdQHw->executeCommandLists(1, &inOrderRegularCmdListHandle, nullptr, false, nullptr, 0, nullptr); + mockCmdQHw->executeCommandLists(1, ®ularHandle, nullptr, false, nullptr, 0, nullptr); verifyPatching(1); - mockCmdQHw->executeCommandLists(1, &inOrderRegularCmdListHandle, nullptr, false); - mockCmdQHw->executeCommandLists(1, ®ularHandle, nullptr, false); + mockCmdQHw->executeCommandLists(1, &inOrderRegularCmdListHandle, nullptr, false, nullptr, 0, nullptr); + mockCmdQHw->executeCommandLists(1, ®ularHandle, nullptr, false, nullptr, 0, nullptr); verifyPatching(2); - mockCmdQHw->executeCommandLists(1, ®ularHandle, nullptr, false); + mockCmdQHw->executeCommandLists(1, ®ularHandle, nullptr, false, nullptr, 0, nullptr); verifyPatching(2); } diff --git a/level_zero/core/test/unit_tests/sources/cmdqueue/test_cmdqueue_1.cpp b/level_zero/core/test/unit_tests/sources/cmdqueue/test_cmdqueue_1.cpp index cf56162ea7..da23fc11c1 100644 --- a/level_zero/core/test/unit_tests/sources/cmdqueue/test_cmdqueue_1.cpp +++ b/level_zero/core/test/unit_tests/sources/cmdqueue/test_cmdqueue_1.cpp @@ -346,7 +346,7 @@ HWTEST_F(CommandQueueCreate, given100CmdListsWhenExecutingThenCommandStreamIsNot } auto sizeBefore = commandQueue->commandStream.getUsed(); - commandQueue->executeCommandLists(numHandles, cmdListHandles, nullptr, false); + commandQueue->executeCommandLists(numHandles, cmdListHandles, nullptr, false, nullptr, 0, nullptr); auto sizeAfter = commandQueue->commandStream.getUsed(); EXPECT_LT(sizeBefore, sizeAfter); @@ -382,7 +382,7 @@ HWTEST2_F(CommandQueueCreate, givenOutOfHostMemoryErrorFromSubmitBatchBufferWhen ze_command_list_handle_t cmdListHandles[1] = {commandList->toHandle()}; - const auto result = commandQueue->executeCommandLists(1, cmdListHandles, nullptr, false); + const auto result = commandQueue->executeCommandLists(1, cmdListHandles, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_ERROR_OUT_OF_HOST_MEMORY, result); commandQueue->destroy(); } @@ -406,7 +406,7 @@ HWTEST2_F(CommandQueueCreate, givenGpuHangInReservingLinearStreamWhenExecutingCo ze_command_list_handle_t cmdListHandles[1] = {commandList->toHandle()}; - const auto result = commandQueue.executeCommandLists(1, cmdListHandles, nullptr, false); + const auto result = commandQueue.executeCommandLists(1, cmdListHandles, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_ERROR_DEVICE_LOST, result); } @@ -473,11 +473,11 @@ HWTEST2_F(CommandQueueCreate, GivenDispatchTaskCountPostSyncRequiredWhenExecuteC commandList->close(); ze_command_list_handle_t cmdListHandle = commandList->toHandle(); commandQueue->dispatchTaskCountPostSyncRequired = false; - commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, false); + commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, false, nullptr, 0, nullptr); auto estimatedSizeWithoutBarrier = commandQueue->requiredSizeCalled; commandQueue->dispatchTaskCountPostSyncRequired = true; - commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, false); + commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, false, nullptr, 0, nullptr); auto estimatedSizeWithtBarrier = commandQueue->requiredSizeCalled; auto sizeForBarrier = NEO::MemorySynchronizationCommands::getSizeForBarrierWithPostSyncOperation(device->getNEODevice()->getRootDeviceEnvironment(), false); @@ -511,7 +511,7 @@ HWTEST_F(CommandQueueCreate, givenUpdateTaskCountFromWaitAndRegularCmdListWhenDi commandList->close(); ze_command_list_handle_t cmdListHandle = commandList->toHandle(); - commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, false); + commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, false, nullptr, 0, nullptr); GenCmdList cmdList; ASSERT_TRUE(FamilyType::Parse::parseCommandBuffer( @@ -552,7 +552,7 @@ HWTEST_F(CommandQueueCreate, givenUpdateTaskCountFromWaitAndImmediateCmdListWhen ASSERT_NE(nullptr, commandList); ze_command_list_handle_t cmdListHandle = commandList->toHandle(); - commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, false); + commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, false, nullptr, 0, nullptr); GenCmdList cmdList; ASSERT_TRUE(FamilyType::Parse::parseCommandBuffer( @@ -756,7 +756,7 @@ TEST_F(CommandQueueCreate, givenCmdQueueWithBlitCopyWhenExecutingCopyBlitCommand commandList->close(); auto commandListHandle = commandList->toHandle(); - auto status = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + auto status = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(status, ZE_RESULT_SUCCESS); @@ -1119,7 +1119,7 @@ HWTEST2_F(ExecuteCommandListTests, givenExecuteCommandListWhenItReturnsThenConta commandList->commandContainer.getSshAllocations().push_back(&graphicsAllocation1); commandList->commandContainer.getSshAllocations().push_back(&graphicsAllocation2); - commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(0u, commandQueue->csr->getResidencyAllocations().size()); EXPECT_EQ(0u, commandQueue->heapContainer.size()); @@ -1144,10 +1144,10 @@ HWTEST2_F(ExecuteCommandListTests, givenRegularCmdListWhenExecutionThenIncSubmis auto commandListHandle = computeCmdList->toHandle(); computeCmdList->close(); - commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(1u, computeCmdList->inOrderExecInfo->getRegularCmdListSubmissionCounter()); - commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(2u, computeCmdList->inOrderExecInfo->getRegularCmdListSubmissionCounter()); } @@ -1160,10 +1160,10 @@ HWTEST2_F(ExecuteCommandListTests, givenRegularCmdListWhenExecutionThenIncSubmis copyCmdList->close(); commandQueue->isCopyOnlyCommandQueue = true; - commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(1u, copyCmdList->inOrderExecInfo->getRegularCmdListSubmissionCounter()); - commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(2u, copyCmdList->inOrderExecInfo->getRegularCmdListSubmissionCounter()); } } @@ -1191,7 +1191,7 @@ HWTEST2_F(ExecuteCommandListTests, givenOutOfMemorySubmitBatchBufferThenExecuteC auto commandListHandle = commandList->toHandle(); commandList->close(); - auto res = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + auto res = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_ERROR_OUT_OF_DEVICE_MEMORY, res); commandQueue->destroy(); @@ -1218,7 +1218,7 @@ HWTEST2_F(CommandQueueDestroy, givenCommandQueueAndCommandListWithSshAndScratchW commandList->commandContainer.getSshAllocations().push_back(&graphicsAllocation1); commandList->commandContainer.getSshAllocations().push_back(&graphicsAllocation2); - commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(commandQueue->mockHeapContainer.size(), 3u); commandQueue->destroy(); @@ -1245,7 +1245,7 @@ HWTEST2_F(CommandQueueDestroy, givenCommandQueueAndCommandListWithSshAndPrivateS commandList->commandContainer.getSshAllocations().push_back(&graphicsAllocation1); commandList->commandContainer.getSshAllocations().push_back(&graphicsAllocation2); - commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(commandQueue->mockHeapContainer.size(), 3u); commandQueue->destroy(); @@ -1269,7 +1269,7 @@ HWTEST2_F(ExecuteCommandListTests, givenBindlessHelperWhenCommandListIsExecutedO auto commandListHandle = commandList->toHandle(); commandList->close(); - commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(commandQueue->mockHeapContainer.size(), 0u); EXPECT_EQ(commandQueue->heapContainer.size(), 0u); @@ -1291,7 +1291,7 @@ HWTEST2_F(ExecuteCommandListTests, givenFailingSubmitBatchBufferThenExecuteComma auto commandListHandle = commandList->toHandle(); commandList->close(); - auto res = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + auto res = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_ERROR_UNKNOWN, res); commandQueue->destroy(); @@ -1319,7 +1319,7 @@ HWTEST2_F(ExecuteCommandListTests, givenFailingSubmitBatchBufferThenResetGraphic commandList->commandContainer.addToResidencyContainer(&graphicsAllocation1); commandList->commandContainer.addToResidencyContainer(&graphicsAllocation2); static_cast *>(csr)->taskCount = 0; - auto res = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + auto res = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_ERROR_UNKNOWN, res); EXPECT_EQ(NEO::GraphicsAllocation::objectNotUsed, graphicsAllocation1.getTaskCount(csr->getOsContext().getContextId())); @@ -1350,7 +1350,7 @@ HWTEST2_F(ExecuteCommandListTests, givenFailingSubmitBatchBufferThenResetGraphic commandList->commandContainer.addToResidencyContainer(&graphicsAllocation1); commandList->commandContainer.addToResidencyContainer(&graphicsAllocation2); static_cast *>(csr)->taskCount = 2; - auto res = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + auto res = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_ERROR_UNKNOWN, res); EXPECT_EQ(2u, graphicsAllocation1.getTaskCount(csr->getOsContext().getContextId())); @@ -1375,7 +1375,7 @@ HWTEST2_F(ExecuteCommandListTests, givenFailingSubmitBatchBufferThenWaitForCompl TaskCountType flushedTaskCountPrior = csr->peekTaskCount(); csr->setLatestFlushedTaskCount(flushedTaskCountPrior); - auto res = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + auto res = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_ERROR_UNKNOWN, res); EXPECT_EQ(csr->peekLatestFlushedTaskCount(), flushedTaskCountPrior); @@ -1396,7 +1396,7 @@ HWTEST2_F(ExecuteCommandListTests, givenSuccessfulSubmitBatchBufferThenExecuteCo auto commandListHandle = commandList->toHandle(); commandList->close(); - auto res = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + auto res = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, res); commandQueue->destroy(); @@ -1429,10 +1429,10 @@ HWTEST2_F(ExecuteCommandListTests, givenCommandQueueHavingTwoB2BCommandListsThen EXPECT_EQ(true, csr->getMediaVFEStateDirty()); EXPECT_EQ(true, csr->getGSBAStateDirty()); - commandQueue->executeCommandLists(1, &commandListHandle0, nullptr, false); + commandQueue->executeCommandLists(1, &commandListHandle0, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(false, csr->getMediaVFEStateDirty()); EXPECT_EQ(false, csr->getGSBAStateDirty()); - commandQueue->executeCommandLists(1, &commandListHandle1, nullptr, false); + commandQueue->executeCommandLists(1, &commandListHandle1, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(false, csr->getMediaVFEStateDirty()); EXPECT_EQ(false, csr->getGSBAStateDirty()); @@ -1468,8 +1468,8 @@ HWTEST2_F(ExecuteCommandListTests, givenCommandQueueHavingTwoB2BCommandListsThen ASSERT_NE(nullptr, commandQueue); - commandQueue->executeCommandLists(1, &commandListHandle0, nullptr, false); - commandQueue->executeCommandLists(1, &commandListHandle1, nullptr, false); + commandQueue->executeCommandLists(1, &commandListHandle0, nullptr, false, nullptr, 0, nullptr); + commandQueue->executeCommandLists(1, &commandListHandle1, nullptr, false, nullptr, 0, nullptr); auto usedSpaceAfter = commandQueue->commandStream.getUsed(); @@ -1510,9 +1510,9 @@ HWTEST2_F(ExecuteCommandListTests, givenTwoCommandQueuesHavingTwoB2BCommandLists auto commandListHandle1 = commandList1->toHandle(); commandList1->close(); - commandQueue->executeCommandLists(1, &commandListHandle0, nullptr, false); + commandQueue->executeCommandLists(1, &commandListHandle0, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(512u, csr->getScratchSpaceController()->getPerThreadScratchSpaceSizeSlot0()); - commandQueue->executeCommandLists(1, &commandListHandle1, nullptr, false); + commandQueue->executeCommandLists(1, &commandListHandle1, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(512u, csr->getScratchSpaceController()->getPerThreadScratchSpaceSizeSlot0()); auto usedSpaceAfter = commandQueue->commandStream.getUsed(); @@ -1543,9 +1543,9 @@ HWTEST2_F(ExecuteCommandListTests, givenTwoCommandQueuesHavingTwoB2BCommandLists false, returnValue)); - commandQueue1->executeCommandLists(1, &commandListHandle0, nullptr, false); + commandQueue1->executeCommandLists(1, &commandListHandle0, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(512u, csr->getScratchSpaceController()->getPerThreadScratchSpaceSizeSlot0()); - commandQueue1->executeCommandLists(1, &commandListHandle1, nullptr, false); + commandQueue1->executeCommandLists(1, &commandListHandle1, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(512u, csr->getScratchSpaceController()->getPerThreadScratchSpaceSizeSlot0()); usedSpaceAfter = commandQueue1->commandStream.getUsed(); @@ -1588,9 +1588,9 @@ HWTEST2_F(ExecuteCommandListTests, givenTwoCommandQueuesHavingTwoB2BCommandLists auto commandListHandle1 = commandList1->toHandle(); commandList1->close(); - commandQueue->executeCommandLists(1, &commandListHandle0, nullptr, false); + commandQueue->executeCommandLists(1, &commandListHandle0, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(0u, csr->getScratchSpaceController()->getPerThreadScratchSpaceSizeSlot0()); - commandQueue->executeCommandLists(1, &commandListHandle1, nullptr, false); + commandQueue->executeCommandLists(1, &commandListHandle1, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(512u, csr->getScratchSpaceController()->getPerThreadScratchSpaceSizeSlot0()); auto usedSpaceAfter = commandQueue->commandStream.getUsed(); @@ -1621,9 +1621,9 @@ HWTEST2_F(ExecuteCommandListTests, givenTwoCommandQueuesHavingTwoB2BCommandLists false, returnValue)); - commandQueue1->executeCommandLists(1, &commandListHandle0, nullptr, false); + commandQueue1->executeCommandLists(1, &commandListHandle0, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(512u, csr->getScratchSpaceController()->getPerThreadScratchSpaceSizeSlot0()); - commandQueue1->executeCommandLists(1, &commandListHandle1, nullptr, false); + commandQueue1->executeCommandLists(1, &commandListHandle1, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(512u, csr->getScratchSpaceController()->getPerThreadScratchSpaceSizeSlot0()); usedSpaceAfter = commandQueue1->commandStream.getUsed(); @@ -1666,9 +1666,9 @@ HWTEST2_F(ExecuteCommandListTests, givenTwoCommandQueuesHavingTwoB2BCommandLists auto commandListHandle1 = commandList1->toHandle(); commandList1->close(); - commandQueue->executeCommandLists(1, &commandListHandle0, nullptr, false); + commandQueue->executeCommandLists(1, &commandListHandle0, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(512u, csr->getScratchSpaceController()->getPerThreadScratchSpaceSizeSlot0()); - commandQueue->executeCommandLists(1, &commandListHandle1, nullptr, false); + commandQueue->executeCommandLists(1, &commandListHandle1, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(512u, csr->getScratchSpaceController()->getPerThreadScratchSpaceSizeSlot0()); auto usedSpaceAfter = commandQueue->commandStream.getUsed(); @@ -1699,9 +1699,9 @@ HWTEST2_F(ExecuteCommandListTests, givenTwoCommandQueuesHavingTwoB2BCommandLists false, returnValue)); - commandQueue1->executeCommandLists(1, &commandListHandle0, nullptr, false); + commandQueue1->executeCommandLists(1, &commandListHandle0, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(1024u, csr->getScratchSpaceController()->getPerThreadScratchSpaceSizeSlot0()); - commandQueue1->executeCommandLists(1, &commandListHandle1, nullptr, false); + commandQueue1->executeCommandLists(1, &commandListHandle1, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(1024u, csr->getScratchSpaceController()->getPerThreadScratchSpaceSizeSlot0()); usedSpaceAfter = commandQueue1->commandStream.getUsed(); @@ -1744,9 +1744,9 @@ HWTEST2_F(ExecuteCommandListTests, givenTwoCommandQueuesHavingTwoB2BCommandLists auto commandListHandle1 = commandList1->toHandle(); commandList1->close(); - commandQueue->executeCommandLists(1, &commandListHandle0, nullptr, false); + commandQueue->executeCommandLists(1, &commandListHandle0, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(0u, csr->getScratchSpaceController()->getPerThreadScratchSpaceSizeSlot0()); - commandQueue->executeCommandLists(1, &commandListHandle1, nullptr, false); + commandQueue->executeCommandLists(1, &commandListHandle1, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(512u, csr->getScratchSpaceController()->getPerThreadScratchSpaceSizeSlot0()); auto usedSpaceAfter = commandQueue->commandStream.getUsed(); @@ -1776,9 +1776,9 @@ HWTEST2_F(ExecuteCommandListTests, givenTwoCommandQueuesHavingTwoB2BCommandLists false, false, returnValue)); - commandQueue1->executeCommandLists(1, &commandListHandle0, nullptr, false); + commandQueue1->executeCommandLists(1, &commandListHandle0, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(1024u, csr->getScratchSpaceController()->getPerThreadScratchSpaceSizeSlot0()); - commandQueue1->executeCommandLists(1, &commandListHandle1, nullptr, false); + commandQueue1->executeCommandLists(1, &commandListHandle1, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(2048u, csr->getScratchSpaceController()->getPerThreadScratchSpaceSizeSlot0()); usedSpaceAfter = commandQueue1->commandStream.getUsed(); @@ -1820,9 +1820,9 @@ HWTEST2_F(ExecuteCommandListTests, givenTwoCommandQueuesHavingTwoB2BCommandLists auto commandListHandle1 = commandList1->toHandle(); commandList1->close(); - commandQueue->executeCommandLists(1, &commandListHandle0, nullptr, false); + commandQueue->executeCommandLists(1, &commandListHandle0, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(0u, csr->getScratchSpaceController()->getPerThreadScratchSizeSlot1()); - commandQueue->executeCommandLists(1, &commandListHandle1, nullptr, false); + commandQueue->executeCommandLists(1, &commandListHandle1, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(512u, csr->getScratchSpaceController()->getPerThreadScratchSizeSlot1()); auto usedSpaceAfter = commandQueue->commandStream.getUsed(); @@ -1850,9 +1850,9 @@ HWTEST2_F(ExecuteCommandListTests, givenTwoCommandQueuesHavingTwoB2BCommandLists false, false, returnValue)); - commandQueue1->executeCommandLists(1, &commandListHandle0, nullptr, false); + commandQueue1->executeCommandLists(1, &commandListHandle0, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(1024u, csr->getScratchSpaceController()->getPerThreadScratchSizeSlot1()); - commandQueue1->executeCommandLists(1, &commandListHandle1, nullptr, false); + commandQueue1->executeCommandLists(1, &commandListHandle1, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(2048u, csr->getScratchSpaceController()->getPerThreadScratchSizeSlot1()); usedSpaceAfter = commandQueue1->commandStream.getUsed(); @@ -1889,7 +1889,7 @@ HWTEST_F(ExecuteCommandListTests, givenDirectSubmissionEnabledWhenExecutingCmdLi auto commandListHandle = commandList->toHandle(); commandList->close(); - commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); auto usedSpaceAfter = commandQueue->commandStream.getUsed(); @@ -1934,7 +1934,7 @@ HWTEST_F(ExecuteCommandListTests, givenDirectSubmissionEnabledAndDebugFlagSetWhe auto commandListHandle = commandList->toHandle(); commandList->close(); - commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); auto usedSpaceAfter = commandQueue->commandStream.getUsed(); diff --git a/level_zero/core/test/unit_tests/sources/cmdqueue/test_cmdqueue_2.cpp b/level_zero/core/test/unit_tests/sources/cmdqueue/test_cmdqueue_2.cpp index b3c0cad83c..a0c229e3ab 100644 --- a/level_zero/core/test/unit_tests/sources/cmdqueue/test_cmdqueue_2.cpp +++ b/level_zero/core/test/unit_tests/sources/cmdqueue/test_cmdqueue_2.cpp @@ -136,7 +136,7 @@ HWTEST_TEMPLATED_F(AubCsrTest, givenAubCsrSyncQueueAndKmdWaitWhenCallingExecuteC auto commandListHandle = commandList->toHandle(); commandList->close(); - queue->executeCommandLists(1, &commandListHandle, nullptr, false); + queue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(aubCsr->pollForCompletionCalled, 1u); L0::CommandQueue::fromHandle(commandQueue)->destroy(); @@ -162,7 +162,7 @@ HWTEST_TEMPLATED_F(AubCsrTest, givenAubCsrAndSyncQueueWhenCallingExecuteCommandL auto commandListHandle = commandList->toHandle(); commandList->close(); - queue->executeCommandLists(1, &commandListHandle, nullptr, false); + queue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(aubCsr->pollForCompletionCalled, 0u); L0::CommandQueue::fromHandle(commandQueue)->destroy(); @@ -188,7 +188,7 @@ HWTEST_TEMPLATED_F(AubCsrTest, givenAubCsrAndAsyncQueueWhenCallingExecuteCommand auto commandListHandle = commandList->toHandle(); commandList->close(); - queue->executeCommandLists(1, &commandListHandle, nullptr, false); + queue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(aubCsr->pollForCompletionCalled, 0u); L0::CommandQueue::fromHandle(commandQueue)->destroy(); @@ -385,7 +385,7 @@ HWTEST2_F(MultiTileCommandQueueSynchronizeTest, givenMultiplePartitionCountWhenC ze_command_list_handle_t cmdListHandle = commandList->toHandle(); commandList->close(); - returnValue = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, false); + returnValue = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(returnValue, ZE_RESULT_SUCCESS); uint64_t timeout = std::numeric_limits::max(); @@ -427,7 +427,7 @@ HWTEST2_F(MultiTileCommandQueueSynchronizeTest, givenCsrHasMultipleActivePartiti ze_command_list_handle_t cmdListHandle = commandList->toHandle(); commandList->close(); - commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, false); + commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(returnValue, ZE_RESULT_SUCCESS); EXPECT_EQ(2u, commandQueue->partitionCount); @@ -512,12 +512,12 @@ HWTEST_F(CommandQueueSynchronizeTest, givenSynchronousCommandQueueWhenTagUpdateF ze_command_list_handle_t cmdListHandle = commandList->toHandle(); commandList->close(); - returnValue = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, false); + returnValue = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, returnValue); auto usedSpaceBefore = commandQueue->commandStream.getUsed(); - returnValue = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, false); + returnValue = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, returnValue); auto usedSpaceAfter = commandQueue->commandStream.getUsed(); @@ -803,7 +803,7 @@ HWTEST2_F(DeviceWithDualStorage, givenCmdListWithAppendedKernelAndUsmTransferAnd auto sizeBefore = commandQueue->commandStream.getUsed(); auto pageFaultSizeBefore = pageFaultCmdQueue->commandStream.getUsed(); auto handle = commandList->toHandle(); - commandQueue->executeCommandLists(1, &handle, nullptr, true); + commandQueue->executeCommandLists(1, &handle, nullptr, true, nullptr, 0, nullptr); auto sizeAfter = commandQueue->commandStream.getUsed(); auto pageFaultSizeAfter = pageFaultCmdQueue->commandStream.getUsed(); EXPECT_LT(sizeBefore, sizeAfter); diff --git a/level_zero/core/test/unit_tests/sources/cmdqueue/test_cmdqueue_3.cpp b/level_zero/core/test/unit_tests/sources/cmdqueue/test_cmdqueue_3.cpp index be64669d85..2d022c2b5d 100644 --- a/level_zero/core/test/unit_tests/sources/cmdqueue/test_cmdqueue_3.cpp +++ b/level_zero/core/test/unit_tests/sources/cmdqueue/test_cmdqueue_3.cpp @@ -311,7 +311,7 @@ HWTEST_F(CommandQueueCommandsSingleTile, givenCommandQueueWhenExecutingCommandLi auto commandListHandle = commandList->toHandle(); commandList->close(); - auto status = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + auto status = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); auto globalFence = csr.getGlobalFenceAllocation(); if (globalFence) { @@ -361,7 +361,7 @@ HWTEST2_F(CommandQueueCommandsMultiTile, givenCommandQueueOnMultiTileWhenExecuti auto commandListHandle = commandList->toHandle(); auto workPartitionAllocation = csr.getWorkPartitionAllocation(); csr.expectedGa = workPartitionAllocation; - auto status = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + auto status = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(status, ZE_RESULT_SUCCESS); EXPECT_EQ(2u, csr.activePartitionsConfig); @@ -451,7 +451,7 @@ HWTEST_F(CommandQueueIndirectAllocations, givenDebugModeToTreatIndirectAllocatio EXPECT_FALSE(gpuAlloc->isResident(csr.getOsContext().getContextId())); - result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); EXPECT_TRUE(gpuAlloc->isResident(csr.getOsContext().getContextId())); @@ -516,7 +516,7 @@ HWTEST_F(CommandQueueIndirectAllocations, givenDeviceThatSupportsSubmittingIndir static_cast(driverHandle->getMemoryManager())->overrideAllocateAsPackReturn = 1u; - result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); EXPECT_TRUE(gpuAlloc->isResident(csr.getOsContext().getContextId())); @@ -718,7 +718,7 @@ HWTEST2_F(EngineInstancedDeviceExecuteTests, givenEngineInstancedDeviceWhenExecu auto commandList = std::unique_ptr(CommandList::whiteboxCast(CommandList::create(productFamily, l0Device, NEO::EngineGroupType::compute, 0u, returnValue, false))); auto commandListHandle = commandList->toHandle(); commandList->close(); - commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); GenCmdList cmdList; FamilyType::Parse::parseCommandBuffer(cmdList, commandQueue->commandStream.getCpuBase(), commandQueue->commandStream.getUsed()); @@ -769,7 +769,7 @@ HWTEST2_F(EngineInstancedDeviceExecuteTests, givenEngineInstancedDeviceWithFabri auto commandList = std::unique_ptr(CommandList::whiteboxCast(CommandList::create(productFamily, l0Device, NEO::EngineGroupType::compute, 0u, returnValue, false))); auto commandListHandle = commandList->toHandle(); commandList->close(); - commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); GenCmdList cmdList; FamilyType::Parse::parseCommandBuffer(cmdList, commandQueue->commandStream.getCpuBase(), commandQueue->commandStream.getUsed()); @@ -824,7 +824,7 @@ HWTEST2_F(CommandQueueIndirectAllocations, givenCtxWithIndirectAccessWhenExecuti ctx.hasIndirectAccess = true; ctx.isDispatchTaskCountPostSyncRequired = false; - commandQueue->executeCommandListsRegular(ctx, 1, &cmdListHandle, nullptr); + commandQueue->executeCommandListsRegular(ctx, 1, &cmdListHandle, nullptr, nullptr, 0, nullptr); EXPECT_EQ(commandQueue->handleIndirectAllocationResidencyCalledTimes, 1u); commandQueue->destroy(); } @@ -850,7 +850,7 @@ HWTEST2_F(CommandQueueIndirectAllocations, givenCtxWitNohIndirectAccessWhenExecu ctx.hasIndirectAccess = false; ctx.isDispatchTaskCountPostSyncRequired = false; - commandQueue->executeCommandListsRegular(ctx, 1, &cmdListHandle, nullptr); + commandQueue->executeCommandListsRegular(ctx, 1, &cmdListHandle, nullptr, nullptr, 0, nullptr); EXPECT_EQ(commandQueue->handleIndirectAllocationResidencyCalledTimes, 0u); commandQueue->destroy(); } @@ -1166,7 +1166,7 @@ HWTEST2_F(CommandQueueTest, whenExecuteCommandListsIsCalledThenCorrectSizeOfFron calculatedSize = estimateAllCommmandLists(commandQueue, csr, commandLists, commandListSize, true); EXPECT_EQ(1 * singleFrontEndCmdSize, calculatedSize); - commandQueue->executeCommandLists(4, commandLists, nullptr, false); + commandQueue->executeCommandLists(4, commandLists, nullptr, false, nullptr, 0, nullptr); } int32_t expectedComputeDispatchAllWalkerEnable = fePropertiesSupport.computeDispatchAllWalker ? 0 : -1; expectedSingleFrontEndSizeNumber = fePropertiesSupport.computeDispatchAllWalker ? 1 : 0; @@ -1180,7 +1180,7 @@ HWTEST2_F(CommandQueueTest, whenExecuteCommandListsIsCalledThenCorrectSizeOfFron calculatedSize = estimateAllCommmandLists(commandQueue, csr, commandLists, commandListSize, true); EXPECT_EQ((expectedSingleFrontEndSizeNumber + 1) * singleFrontEndCmdSize, calculatedSize); - commandQueue->executeCommandLists(3, commandLists, nullptr, false); + commandQueue->executeCommandLists(3, commandLists, nullptr, false, nullptr, 0, nullptr); } EXPECT_EQ(expectedComputeDispatchAllWalkerEnable, csr->getStreamProperties().frontEndState.computeDispatchAllWalkerEnable.value); { @@ -1202,7 +1202,7 @@ HWTEST2_F(CommandQueueTest, whenExecuteCommandListsIsCalledThenCorrectSizeOfFron calculatedSize = estimateAllCommmandLists(commandQueue, csr, commandLists, commandListSize, true); EXPECT_EQ(1 * singleFrontEndCmdSize, calculatedSize); - commandQueue->executeCommandLists(1, commandLists, nullptr, false); + commandQueue->executeCommandLists(1, commandLists, nullptr, false, nullptr, 0, nullptr); } expectedComputeDispatchAllWalkerEnable = fePropertiesSupport.computeDispatchAllWalker ? 1 : -1; EXPECT_EQ(expectedComputeDispatchAllWalkerEnable, csr->getStreamProperties().frontEndState.computeDispatchAllWalkerEnable.value); @@ -1215,7 +1215,7 @@ HWTEST2_F(CommandQueueTest, whenExecuteCommandListsIsCalledThenCorrectSizeOfFron calculatedSize = estimateAllCommmandLists(commandQueue, csr, commandLists, commandListSize, true); EXPECT_EQ(1 * singleFrontEndCmdSize, calculatedSize); - commandQueue->executeCommandLists(1, commandLists, nullptr, false); + commandQueue->executeCommandLists(1, commandLists, nullptr, false, nullptr, 0, nullptr); } expectedComputeDispatchAllWalkerEnable = fePropertiesSupport.computeDispatchAllWalker ? 0 : -1; EXPECT_EQ(expectedComputeDispatchAllWalkerEnable, csr->getStreamProperties().frontEndState.computeDispatchAllWalkerEnable.value); @@ -1247,7 +1247,7 @@ HWTEST2_F(CommandQueueTest, givenRegularKernelScheduledAsCooperativeWhenExecuteC EXPECT_EQ(-1, csr->getStreamProperties().frontEndState.computeDispatchAllWalkerEnable.value); ze_command_list_handle_t commandLists[] = {commandList->toHandle()}; - commandQueue->executeCommandLists(1, commandLists, nullptr, false); + commandQueue->executeCommandLists(1, commandLists, nullptr, false, nullptr, 0, nullptr); NEO::FrontEndPropertiesSupport fePropertiesSupport = {}; auto &productHelper = device->getProductHelper(); productHelper.fillFrontEndPropertiesSupportStructure(fePropertiesSupport, device->getHwInfo()); @@ -1306,24 +1306,24 @@ HWTEST2_F(CommandQueueTest, givenTwoCommandQueuesUsingOneCsrWhenExecuteCommandLi int32_t expectedCurrentState = dispatchAllWalkerSupport ? 0 : -1; - commandQueue1->executeCommandLists(1, commandListsA, nullptr, false); + commandQueue1->executeCommandLists(1, commandListsA, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(expectedCurrentState, currentStreamValue); - commandQueue2->executeCommandLists(1, commandListsA, nullptr, false); + commandQueue2->executeCommandLists(1, commandListsA, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(expectedCurrentState, currentStreamValue); - commandQueue2->executeCommandLists(1, commandListsB, nullptr, false); + commandQueue2->executeCommandLists(1, commandListsB, nullptr, false, nullptr, 0, nullptr); expectedCurrentState = expectedCurrentState != -1 ? 1 : -1; EXPECT_EQ(expectedCurrentState, currentStreamValue); - commandQueue1->executeCommandLists(1, commandListsB, nullptr, false); + commandQueue1->executeCommandLists(1, commandListsB, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(expectedCurrentState, currentStreamValue); - commandQueue2->executeCommandLists(1, commandListsA, nullptr, false); + commandQueue2->executeCommandLists(1, commandListsA, nullptr, false, nullptr, 0, nullptr); expectedCurrentState = expectedCurrentState != -1 ? 0 : -1; EXPECT_EQ(expectedCurrentState, currentStreamValue); - commandQueue1->executeCommandLists(1, commandListsB, nullptr, false); + commandQueue1->executeCommandLists(1, commandListsB, nullptr, false, nullptr, 0, nullptr); expectedCurrentState = expectedCurrentState != -1 ? 1 : -1; EXPECT_EQ(expectedCurrentState, currentStreamValue); diff --git a/level_zero/core/test/unit_tests/sources/cmdqueue/test_cmdqueue_debugger.cpp b/level_zero/core/test/unit_tests/sources/cmdqueue/test_cmdqueue_debugger.cpp index e0b9cb8007..e96dd0b930 100644 --- a/level_zero/core/test/unit_tests/sources/cmdqueue/test_cmdqueue_debugger.cpp +++ b/level_zero/core/test/unit_tests/sources/cmdqueue/test_cmdqueue_debugger.cpp @@ -1,5 +1,5 @@ /* - * Copyright (C) 2023 Intel Corporation + * Copyright (C) 2023-2024 Intel Corporation * * SPDX-License-Identifier: MIT * @@ -58,7 +58,7 @@ HWTEST_F(L0CmdQueueDebuggerTest, givenDebuggingEnabledWhenCmdListRequiringSbaPro ze_command_list_handle_t commandListHandle = commandList->toHandle(); const uint32_t numCommandLists = 1u; - result = cmdQ->executeCommandLists(numCommandLists, &commandListHandle, nullptr, true); + result = cmdQ->executeCommandLists(numCommandLists, &commandListHandle, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); auto usedSpaceAfter = cmdStream.getUsed(); diff --git a/level_zero/core/test/unit_tests/sources/cmdqueue/test_cmdqueue_enqueue_cmdlist.cpp b/level_zero/core/test/unit_tests/sources/cmdqueue/test_cmdqueue_enqueue_cmdlist.cpp index 4eaf6985f9..0e57c83b79 100644 --- a/level_zero/core/test/unit_tests/sources/cmdqueue/test_cmdqueue_enqueue_cmdlist.cpp +++ b/level_zero/core/test/unit_tests/sources/cmdqueue/test_cmdqueue_enqueue_cmdlist.cpp @@ -131,7 +131,7 @@ HWTEST_F(CommandQueueExecuteCommandLists, whenACommandListExecutedRequiresUncach auto commandList2 = CommandList::whiteboxCast(CommandList::fromHandle(commandLists[1])); commandList1->requiresQueueUncachedMocs = true; commandList2->requiresQueueUncachedMocs = true; - auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); commandQueue->destroy(); } @@ -157,7 +157,7 @@ HWTEST_F(CommandQueueExecuteCommandLists, givenCommandListThatRequiresDisabledEU auto commandList1 = static_cast(CommandList::fromHandle(commandLists[0])); commandList1->requiredStreamState.frontEndState.disableEUFusion.set(true); - auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); auto &productHelper = device->getProductHelper(); bool disableEuFusion = productHelper.getFrontEndPropertyDisableEuFusionSupport(); @@ -186,7 +186,7 @@ HWTEST_F(CommandQueueExecuteCommandLists, whenASecondLevelBatchBufferPerCommandL auto usedSpaceBefore = commandQueue->commandStream.getUsed(); - auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); auto usedSpaceAfter = commandQueue->commandStream.getUsed(); @@ -241,7 +241,7 @@ HWTEST_F(CommandQueueExecuteCommandLists, givenFenceWhenExecutingCmdListThenFenc ASSERT_NE(nullptr, fence); EXPECT_EQ(ZE_RESULT_NOT_READY, fence->queryStatus()); - auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, fence, true); + auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, fence, true, nullptr, 0, nullptr); *csr.tagAddress = 11; ASSERT_EQ(ZE_RESULT_SUCCESS, result); EXPECT_EQ(*csr.tagAddress, fence->taskCount); @@ -281,7 +281,7 @@ HWTEST2_F(CommandQueueExecuteCommandLists, whenUsingFenceThenExpectEndingPipeCon auto usedSpaceBefore = commandQueue->commandStream.getUsed(); - auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, fenceHandle, true); + auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, fenceHandle, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); @@ -328,7 +328,7 @@ HWTEST_F(CommandQueueExecuteCommandLists, whenExecutingCommandListsThenEndingPip auto usedSpaceBefore = commandQueue->commandStream.getUsed(); - auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); auto usedSpaceAfter = commandQueue->commandStream.getUsed(); @@ -375,7 +375,7 @@ HWTEST2_F(CommandQueueExecuteCommandLists, givenCommandQueueHaving2CommandListsT ASSERT_NE(nullptr, commandQueue); auto usedSpaceBefore = commandQueue->commandStream.getUsed(); - auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); EXPECT_EQ(1024u, neoDevice->getDefaultEngine().commandStreamReceiver->getScratchSpaceController()->getPerThreadScratchSpaceSizeSlot0()); @@ -401,7 +401,7 @@ HWTEST2_F(CommandQueueExecuteCommandLists, givenCommandQueueHaving2CommandListsT ASSERT_NE(nullptr, commandQueue); usedSpaceBefore = commandQueue->commandStream.getUsed(); - result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); EXPECT_EQ(2048u, neoDevice->getDefaultEngine().commandStreamReceiver->getScratchSpaceController()->getPerThreadScratchSpaceSizeSlot0()); @@ -452,7 +452,7 @@ HWTEST_F(CommandQueueExecuteCommandLists, givenMidThreadPreemptionWhenCommandsAr auto usedSpaceBefore = commandQueue->commandStream.getUsed(); - auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); auto usedSpaceAfter = commandQueue->commandStream.getUsed(); @@ -507,7 +507,7 @@ HWTEST2_F(CommandQueueExecuteCommandLists, givenMidThreadPreemptionWhenCommandsA auto usedSpaceBefore = commandQueue->commandStream.getUsed(); - auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); result = commandQueue->synchronize(0); @@ -532,7 +532,7 @@ HWTEST2_F(CommandQueueExecuteCommandLists, givenMidThreadPreemptionWhenCommandsA EXPECT_EQ(cmdList.end(), itorSip); } - result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); result = commandQueue->synchronize(0); @@ -596,7 +596,7 @@ HWTEST2_F(CommandQueueExecuteCommandListsImplicitScalingDisabled, givenCommandLi launchParams.isCooperative = true; pCommandListWithCooperativeKernels->appendLaunchKernelWithParams(&kernel, threadGroupDimensions, nullptr, launchParams); ze_command_list_handle_t commandListCooperative[] = {pCommandListWithCooperativeKernels->toHandle()}; - auto result = pCommandQueue->executeCommandLists(1, commandListCooperative, nullptr, false); + auto result = pCommandQueue->executeCommandLists(1, commandListCooperative, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); EXPECT_EQ(1u, pMockCsr->submitBatchBufferCalled); @@ -606,7 +606,7 @@ HWTEST2_F(CommandQueueExecuteCommandListsImplicitScalingDisabled, givenCommandLi launchParams.isCooperative = false; pCommandListWithNonCooperativeKernels->appendLaunchKernelWithParams(&kernel, threadGroupDimensions, nullptr, launchParams); ze_command_list_handle_t commandListNonCooperative[] = {pCommandListWithNonCooperativeKernels->toHandle()}; - result = pCommandQueue->executeCommandLists(1, commandListNonCooperative, nullptr, false); + result = pCommandQueue->executeCommandLists(1, commandListNonCooperative, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); EXPECT_EQ(2u, pMockCsr->submitBatchBufferCalled); @@ -640,7 +640,7 @@ void CommandQueueExecuteCommandListsFixture::twoCommandListCommandPreemptionTest commandListThreadGroup->toHandle(), commandListDisabled->toHandle()}; uint32_t numCommandLists = sizeof(commandLists) / sizeof(commandLists[0]); - auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); result = commandQueue->synchronize(0); @@ -648,7 +648,7 @@ void CommandQueueExecuteCommandListsFixture::twoCommandListCommandPreemptionTest EXPECT_EQ(NEO::PreemptionMode::Disabled, currentCsr->getPreemptionMode()); - result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); EXPECT_EQ(NEO::PreemptionMode::Disabled, currentCsr->getPreemptionMode()); @@ -931,7 +931,7 @@ HWTEST_F(CommandQueueExecuteCommandLists, GivenCopyCommandQueueWhenExecutingCopy EXPECT_TRUE(commandQueue->peekIsCopyOnlyCommandQueue()); zet_command_list_handle_t cmdListHandle = commandList->toHandle(); - returnValue = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, false); + returnValue = commandQueue->executeCommandLists(1, &cmdListHandle, nullptr, false, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, returnValue); size_t usedSpaceAfter = commandQueue->commandStream.getUsed(); @@ -1005,7 +1005,7 @@ HWTEST_F(CommandQueueExecuteCommandListSWTagsTests, givenEnableSWTagsWhenExecuti auto usedSpaceBefore = commandQueue->commandStream.getUsed(); - auto result = commandQueue->executeCommandLists(1, commandLists, nullptr, false); + auto result = commandQueue->executeCommandLists(1, commandLists, nullptr, false, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); auto usedSpaceAfter = commandQueue->commandStream.getUsed(); @@ -1031,7 +1031,7 @@ HWTEST_F(CommandQueueExecuteCommandListSWTagsTests, givenEnableSWTagsAndCommandL CommandList::whiteboxCast(CommandList::fromHandle(commandLists[0]))->commandListPreemptionMode = PreemptionMode::Disabled; auto usedSpaceBefore = commandQueue->commandStream.getUsed(); - auto result = commandQueue->executeCommandLists(1, commandLists, nullptr, false); + auto result = commandQueue->executeCommandLists(1, commandLists, nullptr, false, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); auto usedSpaceAfter = commandQueue->commandStream.getUsed(); @@ -1134,7 +1134,7 @@ HWTEST2_F(MultiDeviceCommandQueueExecuteCommandLists, givenMultiplePartitionCoun // 1st execute call initialized pipeline auto usedSpaceBefore1stExecute = commandQueue->commandStream.getUsed(); - auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, fenceHandle, true); + auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, fenceHandle, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, returnValue); auto usedSpaceOn1stExecute = commandQueue->commandStream.getUsed() - usedSpaceBefore1stExecute; @@ -1144,7 +1144,7 @@ HWTEST2_F(MultiDeviceCommandQueueExecuteCommandLists, givenMultiplePartitionCoun findPartitionRegister(cmdList, true); auto usedSpaceBefore2ndExecute = commandQueue->commandStream.getUsed(); - result = commandQueue->executeCommandLists(numCommandLists, commandLists, fenceHandle, true); + result = commandQueue->executeCommandLists(numCommandLists, commandLists, fenceHandle, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); auto usedSpaceAfter2ndExecute = commandQueue->commandStream.getUsed(); ASSERT_GT(usedSpaceAfter2ndExecute, usedSpaceBefore2ndExecute); @@ -1160,7 +1160,7 @@ HWTEST2_F(MultiDeviceCommandQueueExecuteCommandLists, givenMultiplePartitionCoun findPartitionRegister(cmdList, false); auto usedSpaceBefore3rdExecute = commandQueue->commandStream.getUsed(); - result = commandQueue->executeCommandLists(numCommandLists, commandLists, fenceHandle, true); + result = commandQueue->executeCommandLists(numCommandLists, commandLists, fenceHandle, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); auto usedSpaceAfter3rdExecute = commandQueue->commandStream.getUsed(); ASSERT_GT(usedSpaceAfter3rdExecute, usedSpaceBefore3rdExecute); @@ -1221,7 +1221,7 @@ HWTEST_F(CommandQueueExecuteCommandLists, GivenUpdateTaskCountFromWaitWhenExecut ze_fence_handle_t fenceHandle = fence->toHandle(); zet_command_list_handle_t cmdListHandle = commandList->toHandle(); - returnValue = commandQueue->executeCommandLists(1, &cmdListHandle, fenceHandle, false); + returnValue = commandQueue->executeCommandLists(1, &cmdListHandle, fenceHandle, false, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, returnValue); size_t usedSpaceAfter = commandQueue->commandStream.getUsed(); @@ -1274,7 +1274,7 @@ HWTEST_F(CommandQueueExecuteCommandLists, GivenCopyCommandQueueWhenExecutingCopy ze_fence_handle_t fenceHandle = fence->toHandle(); zet_command_list_handle_t cmdListHandle = commandList->toHandle(); - returnValue = commandQueue->executeCommandLists(1, &cmdListHandle, fenceHandle, false); + returnValue = commandQueue->executeCommandLists(1, &cmdListHandle, fenceHandle, false, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, returnValue); size_t usedSpaceAfter = commandQueue->commandStream.getUsed(); diff --git a/level_zero/core/test/unit_tests/sources/cmdqueue/test_cmdqueue_enqueue_cmdlist_2.cpp b/level_zero/core/test/unit_tests/sources/cmdqueue/test_cmdqueue_enqueue_cmdlist_2.cpp index e94ebcd866..91cddc77e9 100644 --- a/level_zero/core/test/unit_tests/sources/cmdqueue/test_cmdqueue_enqueue_cmdlist_2.cpp +++ b/level_zero/core/test/unit_tests/sources/cmdqueue/test_cmdqueue_enqueue_cmdlist_2.cpp @@ -34,7 +34,7 @@ HWTEST2_F(CommandQueueExecuteCommandListsSimpleTest, GivenSynchronousModeWhenExe ze_command_list_handle_t commandLists[] = { CommandList::create(productFamily, device, NEO::EngineGroupType::renderCompute, 0u, returnValue, false)->toHandle()}; CommandList::fromHandle(commandLists[0])->close(); - mockCmdQ->executeCommandLists(1, commandLists, nullptr, true); + mockCmdQ->executeCommandLists(1, commandLists, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(mockCmdQ->synchronizedCalled, 1u); CommandList::fromHandle(commandLists[0])->destroy(); mockCmdQ->destroy(); @@ -52,7 +52,7 @@ HWTEST2_F(CommandQueueExecuteCommandListsSimpleTest, GivenSynchronousModeAndDevi ze_command_list_handle_t commandLists[] = { CommandList::create(productFamily, device, NEO::EngineGroupType::renderCompute, 0u, returnValue, false)->toHandle()}; CommandList::fromHandle(commandLists[0])->close(); - const auto result = mockCmdQ->executeCommandLists(1, commandLists, nullptr, true); + const auto result = mockCmdQ->executeCommandLists(1, commandLists, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(mockCmdQ->synchronizedCalled, 1u); EXPECT_EQ(ZE_RESULT_ERROR_DEVICE_LOST, result); @@ -69,7 +69,7 @@ HWTEST2_F(CommandQueueExecuteCommandListsSimpleTest, GivenAsynchronousModeWhenEx ze_command_list_handle_t commandLists[] = { CommandList::create(productFamily, device, NEO::EngineGroupType::renderCompute, 0u, returnValue, false)->toHandle()}; CommandList::fromHandle(commandLists[0])->close(); - mockCmdQ->executeCommandLists(1, commandLists, nullptr, true); + mockCmdQ->executeCommandLists(1, commandLists, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(mockCmdQ->synchronizedCalled, 0u); CommandList::fromHandle(commandLists[0])->destroy(); mockCmdQ->destroy(); @@ -98,7 +98,7 @@ HWTEST2_F(CommandQueueExecuteCommandListsSimpleTest, whenUsingFenceThenLastPipeC uint32_t numCommandLists = sizeof(commandLists) / sizeof(commandLists[0]); CommandList::fromHandle(commandLists[0])->close(); CommandList::fromHandle(commandLists[1])->close(); - auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, fenceHandle, true); + auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, fenceHandle, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); @@ -150,7 +150,7 @@ HWTEST2_F(CommandQueueExecuteCommandListsSimpleTest, givenTwoCommandQueuesUsingS CommandList::fromHandle(commandList)->close(); auto usedSpaceBefore = commandQueue->commandStream.getUsed(); - returnValue = commandQueue->executeCommandLists(1, &commandList, nullptr, false); + returnValue = commandQueue->executeCommandLists(1, &commandList, nullptr, false, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, returnValue); auto usedSpaceAfter = commandQueue->commandStream.getUsed(); ASSERT_GT(usedSpaceAfter, usedSpaceBefore); @@ -175,7 +175,7 @@ HWTEST2_F(CommandQueueExecuteCommandListsSimpleTest, givenTwoCommandQueuesUsingS ASSERT_NE(nullptr, commandQueue2); usedSpaceBefore = commandQueue2->commandStream.getUsed(); - returnValue = commandQueue2->executeCommandLists(1, &commandList, nullptr, false); + returnValue = commandQueue2->executeCommandLists(1, &commandList, nullptr, false, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, returnValue); usedSpaceAfter = commandQueue2->commandStream.getUsed(); ASSERT_GT(usedSpaceAfter, usedSpaceBefore); @@ -213,7 +213,7 @@ HWTEST2_F(CommandQueueExecuteCommandListsSimpleTest, givenTwoCommandQueuesUsingS CommandList::fromHandle(commandList)->close(); auto usedSpaceBefore = commandQueue->commandStream.getUsed(); - returnValue = commandQueue->executeCommandLists(1, &commandList, nullptr, false); + returnValue = commandQueue->executeCommandLists(1, &commandList, nullptr, false, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, returnValue); auto usedSpaceAfter = commandQueue->commandStream.getUsed(); ASSERT_GT(usedSpaceAfter, usedSpaceBefore); @@ -244,7 +244,7 @@ HWTEST2_F(CommandQueueExecuteCommandListsSimpleTest, givenTwoCommandQueuesUsingS ASSERT_NE(nullptr, commandQueue2); usedSpaceBefore = commandQueue2->commandStream.getUsed(); - returnValue = commandQueue2->executeCommandLists(1, &commandList, nullptr, false); + returnValue = commandQueue2->executeCommandLists(1, &commandList, nullptr, false, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, returnValue); usedSpaceAfter = commandQueue2->commandStream.getUsed(); ASSERT_GT(usedSpaceAfter, usedSpaceBefore); @@ -388,7 +388,7 @@ struct PauseOnGpuFixture : public Test { result = commandList->close(); ASSERT_EQ(ZE_RESULT_SUCCESS, result); - result = commandQueue->executeCommandLists(1u, &commandListHandle, nullptr, false); + result = commandQueue->executeCommandLists(1u, &commandListHandle, nullptr, false, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); } @@ -430,7 +430,7 @@ struct PauseOnGpuTests : public PauseOnGpuFixture { result = commandList->close(); ASSERT_EQ(ZE_RESULT_SUCCESS, result); - result = commandQueue->executeCommandLists(1u, &commandListHandle, nullptr, false); + result = commandQueue->executeCommandLists(1u, &commandListHandle, nullptr, false, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); } }; @@ -807,7 +807,7 @@ HWTEST_F(CommandQueueExecuteCommandListsSimpleTest, GivenDirtyFlagForContextInBi uint32_t numCommandLists = sizeof(commandLists) / sizeof(commandLists[0]); CommandList::fromHandle(commandLists[0])->close(); CommandList::fromHandle(commandLists[1])->close(); - auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); @@ -854,7 +854,7 @@ HWTEST_F(CommandQueueExecuteCommandListsSimpleTest, GivenRegisterInstructionCach CommandList::create(productFamily, device, NEO::EngineGroupType::renderCompute, 0u, returnValue, false)->toHandle()}; uint32_t numCommandLists = 1; CommandList::fromHandle(commandLists[0])->close(); - auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); diff --git a/level_zero/core/test/unit_tests/sources/context/test_context.cpp b/level_zero/core/test/unit_tests/sources/context/test_context.cpp index a0b7742d77..0577150c56 100644 --- a/level_zero/core/test/unit_tests/sources/context/test_context.cpp +++ b/level_zero/core/test/unit_tests/sources/context/test_context.cpp @@ -758,7 +758,7 @@ HWTEST_F(ContextMakeMemoryResidentAndMigrationTests, returnValue, false)); auto commandListHandle = commandList->toHandle(); commandList->close(); - res = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, true); + res = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, res); EXPECT_EQ(mockPageFaultManager->moveAllocationToGpuDomainCalledTimes, 1u); @@ -810,7 +810,7 @@ HWTEST2_F(ContextMakeMemoryResidentAndMigrationTests, commandList->close(); auto commandListHandle = commandList->toHandle(); - res = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, true); + res = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(mockPageFaultManager->moveAllocationsWithinUMAllocsManagerToGpuDomainCalled, 1u); @@ -860,7 +860,7 @@ HWTEST_F(ContextMakeMemoryResidentAndMigrationTests, auto commandListHandle = commandList->toHandle(); commandList->close(); - res = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + res = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, res); EXPECT_EQ(mockPageFaultManager->moveAllocationToGpuDomainCalledTimes, 0u); diff --git a/level_zero/core/test/unit_tests/sources/debugger/test_l0_debugger_1.cpp b/level_zero/core/test/unit_tests/sources/debugger/test_l0_debugger_1.cpp index 1ddfe5184b..5f011581c8 100644 --- a/level_zero/core/test/unit_tests/sources/debugger/test_l0_debugger_1.cpp +++ b/level_zero/core/test/unit_tests/sources/debugger/test_l0_debugger_1.cpp @@ -98,7 +98,7 @@ HWTEST_F(L0DebuggerPerContextAddressSpaceTest, givenDebuggingEnabledWhenCommandL commandList->close(); } - auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); auto usedSpaceAfter = commandQueue->commandStream.getUsed(); @@ -174,7 +174,7 @@ HWTEST_F(L0DebuggerPerContextAddressSpaceTest, givenDebuggingEnabledWhenTwoComma auto commandList = CommandList::fromHandle(commandLists[0]); commandList->close(); - returnValue = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + returnValue = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, returnValue); auto usedSpaceAfter = commandQueue->commandStream.getUsed(); @@ -187,7 +187,7 @@ HWTEST_F(L0DebuggerPerContextAddressSpaceTest, givenDebuggingEnabledWhenTwoComma auto stateSipCmds = findAll(cmdList.begin(), cmdList.end()); EXPECT_EQ(1u, stateSipCmds.size()); - returnValue = commandQueue2->executeCommandLists(numCommandLists, commandLists, nullptr, true); + returnValue = commandQueue2->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, returnValue); auto usedSpaceAfter2 = commandQueue2->commandStream.getUsed(); @@ -504,7 +504,7 @@ HWTEST_F(L0DebuggerSimpleTest, givenUseCsrImmediateSubmissionEnabledForRegularCo ASSERT_EQ(ZE_RESULT_SUCCESS, result); commandList->close(); - result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); commandQueue->synchronize(0); @@ -540,7 +540,7 @@ HWTEST_F(L0DebuggerSimpleTest, givenUseCsrImmediateSubmissionDisabledForRegularC ASSERT_EQ(ZE_RESULT_SUCCESS, result); commandList->close(); - result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); commandQueue->synchronize(0); @@ -833,7 +833,7 @@ HWTEST_F(DebuggerWithGlobalBindlessTest, GivenGlobalBindlessHeapWhenExecutingCmd commandList->close(); memoryOperationsHandler->captureGfxAllocationsForMakeResident = true; - result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); auto allocIter = std::find(memoryOperationsHandler->gfxAllocationsForMakeResident.begin(), diff --git a/level_zero/core/test/unit_tests/sources/debugger/test_l0_debugger_2.cpp b/level_zero/core/test/unit_tests/sources/debugger/test_l0_debugger_2.cpp index 8a19bd4c5f..19b0a894fd 100644 --- a/level_zero/core/test/unit_tests/sources/debugger/test_l0_debugger_2.cpp +++ b/level_zero/core/test/unit_tests/sources/debugger/test_l0_debugger_2.cpp @@ -1,5 +1,5 @@ /* - * Copyright (C) 2021-2023 Intel Corporation + * Copyright (C) 2021-2024 Intel Corporation * * SPDX-License-Identifier: MIT * @@ -444,7 +444,7 @@ HWTEST2_P(L0DebuggerWithBlitterTest, givenUseCsrImmediateSubmissionEnabledForReg ASSERT_EQ(ZE_RESULT_SUCCESS, result); commandList->close(); - result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); commandQueue->synchronize(0); @@ -520,7 +520,7 @@ HWTEST2_P(L0DebuggerWithBlitterTest, givenDebuggingEnabledWhenInternalCmdQIsUsed uint32_t numCommandLists = sizeof(commandLists) / sizeof(commandLists[0]); auto commandList = CommandList::fromHandle(commandLists[0]); - auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); auto sbaBuffer = device->getL0Debugger()->getSbaTrackingBuffer(neoDevice->getDefaultEngine().commandStreamReceiver->getOsContext().getContextId()); @@ -582,7 +582,7 @@ HWTEST_P(L0DebuggerWithBlitterTest, givenDebuggingEnabledWhenCommandListIsExecut ASSERT_EQ(ZE_RESULT_SUCCESS, result); commandList->close(); - result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); auto usedSpaceAfter = commandQueue->commandStream.getUsed(); diff --git a/level_zero/core/test/unit_tests/sources/debugger/test_l0_debugger_sba_tracking.cpp b/level_zero/core/test/unit_tests/sources/debugger/test_l0_debugger_sba_tracking.cpp index f7afdbf85e..387a23b983 100644 --- a/level_zero/core/test/unit_tests/sources/debugger/test_l0_debugger_sba_tracking.cpp +++ b/level_zero/core/test/unit_tests/sources/debugger/test_l0_debugger_sba_tracking.cpp @@ -143,7 +143,7 @@ HWTEST2_F(L0DebuggerPerContextAddressSpaceTest, givenDebuggingEnabledAndRequired uint32_t numCommandLists = sizeof(commandLists) / sizeof(commandLists[0]); - auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); auto usedSpaceAfter = commandQueue->commandStream.getUsed(); @@ -194,7 +194,7 @@ HWTEST2_F(L0DebuggerTest, givenDebuggingEnabledAndDebuggerLogsWhenCommandQueueIs auto commandList = CommandList::fromHandle(commandLists[0]); commandList->close(); - auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); commandQueue->synchronize(0); @@ -231,7 +231,7 @@ HWTEST2_F(L0DebuggerSimpleTest, givenNullL0DebuggerAndDebuggerLogsWhenCommandQue auto commandList = CommandList::fromHandle(commandLists[0]); commandList->close(); - auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); commandQueue->synchronize(0); @@ -263,7 +263,7 @@ HWTEST2_F(L0DebuggerTest, givenL0DebuggerAndDebuggerLogsDisabledWhenCommandQueue auto commandList = CommandList::fromHandle(commandLists[0]); commandList->close(); - auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); commandQueue->synchronize(0); @@ -349,7 +349,7 @@ HWTEST2_F(L0DebuggerTest, givenDebuggingEnabledWhenCommandListIsExecutedThenSbaB auto commandList = CommandList::fromHandle(commandLists[0]); commandList->close(); - auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); auto sbaBuffer = device->getL0Debugger()->getSbaTrackingBuffer(neoDevice->getDefaultEngine().commandStreamReceiver->getOsContext().getContextId()); @@ -426,7 +426,7 @@ HWTEST2_F(L0DebuggerSingleAddressSpace, givenDebuggingEnabledWhenCommandListIsEx auto commandList = CommandList::fromHandle(commandLists[0]); commandList->close(); - auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); auto usedSpaceAfter = commandQueue->commandStream.getUsed(); diff --git a/level_zero/core/test/unit_tests/sources/device/test_l0_device.cpp b/level_zero/core/test/unit_tests/sources/device/test_l0_device.cpp index 0f54d6ba3e..0265830517 100644 --- a/level_zero/core/test/unit_tests/sources/device/test_l0_device.cpp +++ b/level_zero/core/test/unit_tests/sources/device/test_l0_device.cpp @@ -2887,7 +2887,9 @@ TEST_F(MultipleDevicesTest, givenDeviceFailsExecuteCommandListThenCanAccessPeerR ze_result_t executeCommandLists(uint32_t numCommandLists, ze_command_list_handle_t *phCommandLists, - ze_fence_handle_t hFence, bool performMigration) override { return ZE_RESULT_ERROR_UNKNOWN; } + ze_fence_handle_t hFence, bool performMigration, + ze_event_handle_t hSignalEvent, uint32_t numWaitEvents, + ze_event_handle_t *phWaitEvents) override { return ZE_RESULT_ERROR_UNKNOWN; } }; MockDeviceFail(L0::Device *device) : MockDeviceImp(device->getNEODevice(), static_cast(device->getExecEnvironment())) { @@ -2944,7 +2946,9 @@ TEST_F(MultipleDevicesTest, givenQueryPeerStatsReturningBandwidthZeroAndDeviceFa ze_result_t executeCommandLists(uint32_t numCommandLists, ze_command_list_handle_t *phCommandLists, - ze_fence_handle_t hFence, bool performMigration) override { return ZE_RESULT_ERROR_UNKNOWN; } + ze_fence_handle_t hFence, bool performMigration, + ze_event_handle_t hSignalEvent, uint32_t numWaitEvents, + ze_event_handle_t *phWaitEvents) override { return ZE_RESULT_ERROR_UNKNOWN; } }; MockDeviceFail(L0::Device *device) : MockDeviceImp(device->getNEODevice(), static_cast(device->getExecEnvironment())) { @@ -3002,7 +3006,9 @@ TEST_F(MultipleDevicesTest, givenQueryPeerStatsReturningBandwidthNonZeroAndDevic ze_result_t executeCommandLists(uint32_t numCommandLists, ze_command_list_handle_t *phCommandLists, - ze_fence_handle_t hFence, bool performMigration) override { + ze_fence_handle_t hFence, bool performMigration, + ze_event_handle_t hSignalEvent, uint32_t numWaitEvents, + ze_event_handle_t *phWaitEvents) override { return ZE_RESULT_SUCCESS; } }; diff --git a/level_zero/core/test/unit_tests/xe_hpc_core/test_cmdlist_xe_hpc_core.cpp b/level_zero/core/test/unit_tests/xe_hpc_core/test_cmdlist_xe_hpc_core.cpp index bab135735b..27648d346a 100644 --- a/level_zero/core/test/unit_tests/xe_hpc_core/test_cmdlist_xe_hpc_core.cpp +++ b/level_zero/core/test/unit_tests/xe_hpc_core/test_cmdlist_xe_hpc_core.cpp @@ -1,5 +1,5 @@ /* - * Copyright (C) 2021-2023 Intel Corporation + * Copyright (C) 2021-2024 Intel Corporation * * SPDX-License-Identifier: MIT * @@ -142,7 +142,7 @@ HWTEST2_F(CommandListStatePrefetchXeHpcCore, givenForceMemoryPrefetchForKmdMigra auto commandQueue = CommandQueue::create(productFamily, device, neoDevice->getDefaultEngine().commandStreamReceiver, &queueDesc, false, false, false, returnValue); - result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); auto mockMemoryManager = reinterpret_cast(neoDevice->getMemoryManager()); @@ -178,7 +178,7 @@ HWTEST2_F(CommandListStatePrefetchXeHpcCore, givenNoForceMemoryPrefetchForKmdMig auto commandQueue = CommandQueue::create(productFamily, device, neoDevice->getDefaultEngine().commandStreamReceiver, &queueDesc, false, false, false, returnValue); - result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); auto mockMemoryManager = reinterpret_cast(neoDevice->getMemoryManager()); @@ -214,7 +214,7 @@ HWTEST2_F(CommandListStatePrefetchXeHpcCore, givenEnableBOChunkingPrefetchWhenEx auto commandQueue = CommandQueue::create(productFamily, device, neoDevice->getDefaultEngine().commandStreamReceiver, &queueDesc, false, false, false, returnValue); - result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); auto mockMemoryManager = reinterpret_cast(neoDevice->getMemoryManager()); @@ -532,7 +532,7 @@ HWTEST2_F(CommandListStatePrefetchXeHpcCore, givenAppendMemoryPrefetchForKmdMigr EXPECT_EQ(ZE_RESULT_SUCCESS, result); commandList->close(); - result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); EXPECT_TRUE(memoryManager->setMemPrefetchCalled); @@ -613,7 +613,7 @@ HWTEST2_F(CommandListStatePrefetchXeHpcCore, givenAppendMemoryPrefetchForKmdMigr result = commandList->close(); EXPECT_EQ(ZE_RESULT_SUCCESS, result); - result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, true); + result = commandQueue->executeCommandLists(1, &commandListHandle, nullptr, true, nullptr, 0, nullptr); EXPECT_EQ(ZE_RESULT_SUCCESS, result); EXPECT_TRUE(memoryManager->setMemPrefetchCalled); diff --git a/level_zero/core/test/unit_tests/xe_hpc_core/test_cmdqueue_xe_hpc_core.cpp b/level_zero/core/test/unit_tests/xe_hpc_core/test_cmdqueue_xe_hpc_core.cpp index 686ad0a380..c900404e81 100644 --- a/level_zero/core/test/unit_tests/xe_hpc_core/test_cmdqueue_xe_hpc_core.cpp +++ b/level_zero/core/test/unit_tests/xe_hpc_core/test_cmdqueue_xe_hpc_core.cpp @@ -44,7 +44,7 @@ HWTEST2_F(CommandQueueCommandsXeHpc, givenCommandQueueWhenExecutingCommandListsT auto commandListHandle = commandList->toHandle(); commandList->close(); - commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); auto globalFence = csr.getGlobalFenceAllocation(); @@ -72,7 +72,7 @@ HWTEST2_F(CommandQueueCommandsXeHpc, givenCommandQueueWhenExecutingCommandListsT auto commandListHandle = commandList->toHandle(); commandList->close(); - commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); auto globalFence = csr->getGlobalFenceAllocation(); @@ -103,9 +103,9 @@ HWTEST2_F(CommandQueueCommandsXeHpc, givenCommandQueueWhenExecutingCommandListsF auto commandListHandle = commandList->toHandle(); commandList->close(); - commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); auto usedSpaceAfter1stExecute = commandQueue->commandStream.getUsed(); - commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false); + commandQueue->executeCommandLists(1, &commandListHandle, nullptr, false, nullptr, 0, nullptr); auto usedSpaceOn2ndExecute = commandQueue->commandStream.getUsed() - usedSpaceAfter1stExecute; GenCmdList cmdList; diff --git a/level_zero/core/test/unit_tests/xe_hpg_core/test_cmdqueue_enqueuecommandlist_xe_hpg_core.cpp b/level_zero/core/test/unit_tests/xe_hpg_core/test_cmdqueue_enqueuecommandlist_xe_hpg_core.cpp index a4f21e49ff..3aca3420e9 100644 --- a/level_zero/core/test/unit_tests/xe_hpg_core/test_cmdqueue_enqueuecommandlist_xe_hpg_core.cpp +++ b/level_zero/core/test/unit_tests/xe_hpg_core/test_cmdqueue_enqueuecommandlist_xe_hpg_core.cpp @@ -1,5 +1,5 @@ /* - * Copyright (C) 2021-2023 Intel Corporation + * Copyright (C) 2021-2024 Intel Corporation * * SPDX-License-Identifier: MIT * @@ -41,7 +41,7 @@ XE_HPG_CORETEST_F(CommandQueueExecuteCommandListsXeHpgCore, WhenExecutingCmdList uint32_t numCommandLists = sizeof(commandLists) / sizeof(commandLists[0]); CommandList::fromHandle(commandLists[0])->close(); - auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result); @@ -87,7 +87,7 @@ XE_HPG_CORETEST_F(CommandQueueExecuteCommandListsXeHpgCore, WhenExecutingCmdList uint32_t numCommandLists = sizeof(commandLists) / sizeof(commandLists[0]); CommandList::fromHandle(commandLists[0])->close(); - auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true); + auto result = commandQueue->executeCommandLists(numCommandLists, commandLists, nullptr, true, nullptr, 0, nullptr); ASSERT_EQ(ZE_RESULT_SUCCESS, result);