commit c3c352e60050f3deacad767e429a88dc24b31af0
author Georgios Pinitas <georgios.pinitas@arm.com> Thu Mar 18 10:59:40 2021 +0000
committer Georgios Pinitas <georgios.pinitas@arm.com> Wed Apr 28 17:05:40 2021 +0000
tree ad30a0ba717a742caf5e4dcb9d89389cfdc134b0
parent e2535154fa34ac0290ec3daaa44545be0b2b4606

Add Queue support

Queues are responsible for scheduling operators and performing other
runtime related activities like for example tuning.

Signed-off-by: Georgios Pinitas <georgios.pinitas@arm.com>
Change-Id: I0366d9048470d277b8cbf59fa42f95c0ae57c5c9
Reviewed-on: https://review.mlplatform.org/c/ml/ComputeLibrary/+/5487
Tested-by: Arm Jenkins <bsgcomp@arm.com>
Reviewed-by: Michele Di Giorgio <michele.digiorgio@arm.com>
Reviewed-by: Michalis Spyrou <michalis.spyrou@arm.com>
Comments-Addressed: Arm Jenkins <bsgcomp@arm.com>

src/core/CL/OpenCL.cpp

diff --git a/src/core/CL/OpenCL.cpp b/src/core/CL/OpenCL.cpp
index a7be534..d8c2736 100644
--- a/src/core/CL/OpenCL.cpp
+++ b/src/core/CL/OpenCL.cpp
@@ -91,6 +91,7 @@
     LOAD_FUNCTION_PTR(clCreateContext, handle);
     LOAD_FUNCTION_PTR(clCreateContextFromType, handle);
     LOAD_FUNCTION_PTR(clCreateCommandQueue, handle);
+    LOAD_FUNCTION_PTR(clCreateCommandQueueWithProperties, handle);
     LOAD_FUNCTION_PTR(clGetContextInfo, handle);
     LOAD_FUNCTION_PTR(clBuildProgram, handle);
     LOAD_FUNCTION_PTR(clEnqueueNDRangeKernel, handle);
@@ -293,6 +294,23 @@
     }
 }
 
+cl_command_queue clCreateCommandQueueWithProperties(cl_context                 context,
+                                                    cl_device_id               device,
+                                                    const cl_queue_properties *properties,
+                                                    cl_int                    *errcode_ret)
+{
+    arm_compute::CLSymbols::get().load_default();
+    auto func = arm_compute::CLSymbols::get().clCreateCommandQueueWithProperties_ptr;
+    if(func != nullptr)
+    {
+        return func(context, device, properties, errcode_ret);
+    }
+    else
+    {
+        return nullptr;
+    }
+}
+
 cl_context clCreateContext(
     const cl_context_properties *properties,
     cl_uint                      num_devices,

src/core/cpu/kernels/CpuDirectConvolutionOutputStageKernel.cpp

diff --git a/src/core/cpu/kernels/CpuDirectConvolutionStageKernel.cpp b/src/core/cpu/kernels/CpuDirectConvolutionOutputStageKernel.cpp
similarity index 100%
rename from src/core/cpu/kernels/CpuDirectConvolutionStageKernel.cpp
rename to src/core/cpu/kernels/CpuDirectConvolutionOutputStageKernel.cpp

src/core/cpu/kernels/activation/neon/fp16.cpp

diff --git a/src/core/cpu/kernels/activation/NEON/fp16.cpp b/src/core/cpu/kernels/activation/neon/fp16.cpp
similarity index 100%
rename from src/core/cpu/kernels/activation/NEON/fp16.cpp
rename to src/core/cpu/kernels/activation/neon/fp16.cpp

src/core/cpu/kernels/activation/neon/fp32.cpp

diff --git a/src/core/cpu/kernels/activation/NEON/fp32.cpp b/src/core/cpu/kernels/activation/neon/fp32.cpp
similarity index 100%
rename from src/core/cpu/kernels/activation/NEON/fp32.cpp
rename to src/core/cpu/kernels/activation/neon/fp32.cpp

src/core/cpu/kernels/activation/neon/qasymm8.cpp

diff --git a/src/core/cpu/kernels/activation/NEON/qasymm8.cpp b/src/core/cpu/kernels/activation/neon/qasymm8.cpp
similarity index 100%
rename from src/core/cpu/kernels/activation/NEON/qasymm8.cpp
rename to src/core/cpu/kernels/activation/neon/qasymm8.cpp

src/core/cpu/kernels/activation/neon/qasymm8_signed.cpp

diff --git a/src/core/cpu/kernels/activation/NEON/qasymm8_signed.cpp b/src/core/cpu/kernels/activation/neon/qasymm8_signed.cpp
similarity index 100%
rename from src/core/cpu/kernels/activation/NEON/qasymm8_signed.cpp
rename to src/core/cpu/kernels/activation/neon/qasymm8_signed.cpp

src/core/cpu/kernels/activation/neon/qsymm16.cpp

diff --git a/src/core/cpu/kernels/activation/NEON/qsymm16.cpp b/src/core/cpu/kernels/activation/neon/qsymm16.cpp
similarity index 100%
rename from src/core/cpu/kernels/activation/NEON/qsymm16.cpp
rename to src/core/cpu/kernels/activation/neon/qsymm16.cpp

src/core/cpu/kernels/activation/sve/fp16.cpp

diff --git a/src/core/cpu/kernels/activation/SVE/fp16.cpp b/src/core/cpu/kernels/activation/sve/fp16.cpp
similarity index 100%
rename from src/core/cpu/kernels/activation/SVE/fp16.cpp
rename to src/core/cpu/kernels/activation/sve/fp16.cpp

src/core/cpu/kernels/activation/sve/fp32.cpp

diff --git a/src/core/cpu/kernels/activation/SVE/fp32.cpp b/src/core/cpu/kernels/activation/sve/fp32.cpp
similarity index 100%
rename from src/core/cpu/kernels/activation/SVE/fp32.cpp
rename to src/core/cpu/kernels/activation/sve/fp32.cpp

src/core/cpu/kernels/activation/sve/qasymm8.cpp

diff --git a/src/core/cpu/kernels/activation/SVE/qasymm8.cpp b/src/core/cpu/kernels/activation/sve/qasymm8.cpp
similarity index 100%
rename from src/core/cpu/kernels/activation/SVE/qasymm8.cpp
rename to src/core/cpu/kernels/activation/sve/qasymm8.cpp

src/core/cpu/kernels/activation/sve/qasymm8_signed.cpp

diff --git a/src/core/cpu/kernels/activation/SVE/qasymm8_signed.cpp b/src/core/cpu/kernels/activation/sve/qasymm8_signed.cpp
similarity index 100%
rename from src/core/cpu/kernels/activation/SVE/qasymm8_signed.cpp
rename to src/core/cpu/kernels/activation/sve/qasymm8_signed.cpp

src/core/cpu/kernels/activation/sve/qsymm16.cpp

diff --git a/src/core/cpu/kernels/activation/SVE/qsymm16.cpp b/src/core/cpu/kernels/activation/sve/qsymm16.cpp
similarity index 100%
rename from src/core/cpu/kernels/activation/SVE/qsymm16.cpp
rename to src/core/cpu/kernels/activation/sve/qsymm16.cpp