Remove device enqueue part 16

-delete old unused flags

Related-To: NEO-6559
Signed-off-by: Katarzyna Cencelewska <[email protected]>

Author: kcencele

opencl/source/api/cl_types.h

@@ -22,10 +22,6 @@ struct _cl_accelerator_intel : public ClDispatch {
 struct _cl_command_queue : public ClDispatch {
 };
 
-// device_queue is a type used internally
-struct _device_queue : public _cl_command_queue {
-};
-
 struct _cl_context : public ClDispatch {
     bool isSharedContext = false;
 };

opencl/test/unit_test/command_queue/enqueue_kernel_2_tests.cpp

@@ -666,7 +666,7 @@ HWTEST_P(EnqueueKernelPrintfTest, GivenKernelWithPrintfBlockedByEventWhenEventUn
     EXPECT_STREQ("test", output.c_str());
 }
 
-HWTEST_P(EnqueueKernelPrintfTest, GivenKernelWithImplicitArgsWithoutPrintfInParentKernelBlockedByEventWhenEventUnblockedThenOutputPrinted) {
+HWTEST_P(EnqueueKernelPrintfTest, GivenKernelWithImplicitArgsWhenEventUnblockedThenOutputPrinted) {
     auto userEvent = make_releaseable<UserEvent>(context);
 
     MockKernelWithInternals mockKernel(*pClDevice);

opencl/test/unit_test/test_files/igdrcl.config

@@ -39,8 +39,6 @@ InjectInternalBuildOptions = unk
 OverrideCsrAllocationSize = -1
 ForceL1Caching = -1
 UseKmdMigration = -1
-SchedulerSimulationReturnInstance = 0
-SchedulerGWS = 0
 EnableExperimentalCommandBuffer = 0
 OverrideStatelessMocsIndex = -1
 OverrideMocsIndexForScratchSpace = -1
@@ -56,7 +54,6 @@ EnableDebugBreak = 1
 FlushAllCaches = 0
 MakeEachEnqueueBlocking = 0
 DisableResourceRecycling = 0
-ForceDispatchScheduler = 0
 TrackParentEvents = 0
 RebuildPrecompiledKernels = 0
 LoopAtDriverInit = 0
@@ -79,7 +76,6 @@ LogMemoryObject = 0
 ResidencyDebugEnable = 0
 EventsDebugEnable = 0
 EventsTrackerEnable = 0
-PrintEMDebugInformation = 0
 PrintLWSSizes = 0
 PrintDispatchParameters = 0
 PrintProgramBinaryProcessingTime = 0

shared/source/debug_settings/debug_variables_base.inl

@@ -48,7 +48,6 @@ DECLARE_DEBUG_VARIABLE(bool, FlushAllCaches, false, "pipe controls between enque
 DECLARE_DEBUG_VARIABLE(bool, DoNotFlushCaches, false, "clear all possible cache flush flags from pipe controls between enqueue flush")
 DECLARE_DEBUG_VARIABLE(bool, MakeEachEnqueueBlocking, false, "equivalent of finish after each enqueue")
 DECLARE_DEBUG_VARIABLE(bool, DisableResourceRecycling, false, "when set to true disables resource recycling optimization")
-DECLARE_DEBUG_VARIABLE(bool, ForceDispatchScheduler, false, "dispatches scheduler kernel instead of kernel enqueued")
 DECLARE_DEBUG_VARIABLE(bool, TrackParentEvents, false, "events track their parents")
 DECLARE_DEBUG_VARIABLE(bool, RebuildPrecompiledKernels, false, "forces driver to recompile precompiled kernels from sources")
 DECLARE_DEBUG_VARIABLE(bool, LoopAtDriverInit, false, "Adds endless loop in DebugSettingsManager constructor, useful for debugging.")
@@ -83,8 +82,6 @@ DECLARE_DEBUG_VARIABLE(int64_t, OverrideMultiStoragePlacement, -1, "-1: disable,
 DECLARE_DEBUG_VARIABLE(int64_t, ForceCompressionDisabledForCompressedBlitCopies, -1, "-1: default, 0: disabled, 1: enabled. If compression is required, set AUX_CCS_E, but force CompressionEnable filed. 0 should result in uncompressed read/write")
 DECLARE_DEBUG_VARIABLE(int32_t, ForceL1Caching, -1, "-1: default, 0: disable, 1: enable, When set to true driver will program L1 cache policy for surface state and stateless accessess")
 DECLARE_DEBUG_VARIABLE(int32_t, ForceAuxTranslationEnabled, -1, "-1: default, 0: disabled, 1: enabled")
-DECLARE_DEBUG_VARIABLE(int32_t, SchedulerSimulationReturnInstance, 0, "prints execution model related debug information")
-DECLARE_DEBUG_VARIABLE(int32_t, SchedulerGWS, 0, "Forces gws of scheduler kernel, only multiple of 24 allowed or 0 - default selected")
 DECLARE_DEBUG_VARIABLE(int32_t, EnableExperimentalCommandBuffer, 0, "Enables injection of experimental command buffer")
 DECLARE_DEBUG_VARIABLE(int32_t, OverrideStatelessMocsIndex, -1, "-1: feature inactive, >=0 : following MOCS index will be programmed for stateless accesses in state base address (for regular buffers)")
 DECLARE_DEBUG_VARIABLE(int32_t, OverrideMocsIndexForScratchSpace, -1, "-1: feature inactive, >=0 : following MOCS index will be programmed for stateful accesses in surface state for scratch space")
@@ -203,7 +200,6 @@ DECLARE_DEBUG_VARIABLE(bool, LogWaitingForCompletion, false, "Logs waiting for c
 DECLARE_DEBUG_VARIABLE(bool, ResidencyDebugEnable, false, "enables debug messages and checks for Residency Model")
 DECLARE_DEBUG_VARIABLE(bool, EventsDebugEnable, false, "enables debug messages for events, virtual events, blocked enqueues, events trees etc.")
 DECLARE_DEBUG_VARIABLE(bool, EventsTrackerEnable, false, "enables event graphs dumping")
-DECLARE_DEBUG_VARIABLE(bool, PrintEMDebugInformation, false, "prints execution model related debug information")
 DECLARE_DEBUG_VARIABLE(bool, PrintLWSSizes, false, "prints driver choosen local workgroup sizes")
 DECLARE_DEBUG_VARIABLE(bool, PrintDispatchParameters, false, "prints dispatch paramters of kernels passed to clEnqueueNDRangeKernel")
 DECLARE_DEBUG_VARIABLE(bool, PrintProgramBinaryProcessingTime, false, "prints execution time of Program::processGenBinary() method during program building")