OpenCL interoperability sample (KhronosGroup#326)

* OpenCL interoperability sample

* OpenCL Headers as submodule

* Removed OpenCL from ignore files, removed gradle.properties

* Moved android_hardware_buffer include, added casts, checks, initialization

* Fixed clang format check (include indents, space after 'if')

* OpenCL extensions check, proper loading of extensions functions

* Added prefix to the sample name and a list of potential OpenCL libraries to load.

* Reverted looking for libraries other than libOpenCL.so

Author: PavelRudko-ARM

Diff for: .gitmodules

@@ -50,3 +50,6 @@
 [submodule "third_party/cli11"]
 	path = third_party/cli11
 	url = https://github.com/CLIUtils/CLI11.git
+[submodule "third_party/opencl"]
+	path = third_party/opencl
+	url = https://github.com/KhronosGroup/OpenCL-Headers.git

Diff for: samples/README.md

@@ -223,6 +223,10 @@ Shows how to rebuild the acceleration structure and when to set it to fast rebui
 **Extensions**: [```VK_KHR_external_memory```](https://www.khronos.org/registry/vulkan/specs/1.2-extensions/man/html/VK_KHR_external_memory.html), [```VK_KHR_external_semaphore```](https://www.khronos.org/registry/vulkan/specs/1.2-extensions/man/html/VK_KHR_external_semaphore.html)<br/>
 Render a procedural image using OpenGL and incorporate that rendered content into a Vulkan scene.  Demonstrates using the same backing memory for a texture in both OpenGL and Vulkan and how to synchronize the APIs using shared semaphores and barriers.
 
+### [Arm OpenCL interoperability](./extensions/open_cl_interop)<br/>
+**Extensions**: [```VK_ANDROID_EXTERNAL_MEMORY_ANDROID_HARDWARE_BUFFER_EXTENSION_NAME```](https://www.khronos.org/registry/vulkan/specs/1.2-extensions/man/html/VK_ANDROID_external_memory_android_hardware_buffer.html)<br/>
+This sample demonstrates usage of OpenCL extensions available on Arm devices. Fill a procedural texture using OpenCL and display it using Vulkan. In this sample data sharing between APIs is achieved using Android Hardware Buffers.
+
 ### [Timeline semaphore](./extensions/timeline_semaphore)<br/>
 **Extensions**: [```VK_KHR_timeline_semaphore```](https://www.khronos.org/registry/vulkan/specs/1.2-extensions/man/html/VK_KHR_timeline_semaphore.html)
 Demonstrates various use cases which are enabled with timeline semaphores. The sample implements "Game of Life" in an esoteric way,

Diff for: samples/extensions/open_cl_interop/CMakeLists.txt

@@ -0,0 +1,36 @@
+# Copyright (c) 2021, Arm Limited and Contributors
+#
+# SPDX-License-Identifier: Apache-2.0
+#
+# Licensed under the Apache License, Version 2.0 the "License";
+# you may not use this file except in compliance with the License.
+# You may obtain a copy of the License at
+#
+#     http://www.apache.org/licenses/LICENSE-2.0
+#
+# Unless required by applicable law or agreed to in writing, software
+# distributed under the License is distributed on an "AS IS" BASIS,
+# WITHOUT WARRANTIES OR CONDITIONS OF ANY KIND, either express or implied.
+# See the License for the specific language governing permissions and
+# limitations under the License.
+#
+ 
+# The OpenCL interoperability only works on Android
+get_filename_component(FOLDER_NAME ${CMAKE_CURRENT_LIST_DIR} NAME)
+get_filename_component(PARENT_DIR ${CMAKE_CURRENT_LIST_DIR} PATH)
+get_filename_component(CATEGORY_NAME ${PARENT_DIR} NAME)
+
+if(ANDROID)
+    add_sample_with_tags(
+        ID ${FOLDER_NAME}
+        CATEGORY ${CATEGORY_NAME}
+        AUTHOR "Arm"
+        NAME "Arm OpenCL Interoperability"
+        DESCRIPTION "Example showing sharing resources between OpenCL and Vulkan on Arm devices"
+        TAGS "arm"
+        LIBS opencl
+        FILES
+            open_cl_functions.inl
+            open_cl_utils.h
+            open_cl_utils.cpp)
+endif()

Diff for: samples/extensions/open_cl_interop/images/sample.png

@@ -0,0 +1,49 @@
+/* Copyright (c) 2021, Arm Limited and Contributors
+ *
+ * SPDX-License-Identifier: Apache-2.0
+ *
+ * Licensed under the Apache License, Version 2.0 the "License";
+ * you may not use this file except in compliance with the License.
+ * You may obtain a copy of the License at
+ *
+ *     http://www.apache.org/licenses/LICENSE-2.0
+ *
+ * Unless required by applicable law or agreed to in writing, software
+ * distributed under the License is distributed on an "AS IS" BASIS,
+ * WITHOUT WARRANTIES OR CONDITIONS OF ANY KIND, either express or implied.
+ * See the License for the specific language governing permissions and
+ * limitations under the License.
+ */
+
+// Core OpenCL functions, loaded from libOpenCL.so
+#if !defined(OPENCL_EXPORTED_FUNCTION)
+#define OPENCL_EXPORTED_FUNCTION(fun)
+#endif
+
+OPENCL_EXPORTED_FUNCTION(clCreateContext);
+OPENCL_EXPORTED_FUNCTION(clGetDeviceIDs);
+OPENCL_EXPORTED_FUNCTION(clGetPlatformIDs);
+OPENCL_EXPORTED_FUNCTION(clCreateBuffer);
+OPENCL_EXPORTED_FUNCTION(clReleaseMemObject);
+OPENCL_EXPORTED_FUNCTION(clCreateProgramWithSource);
+OPENCL_EXPORTED_FUNCTION(clBuildProgram);
+OPENCL_EXPORTED_FUNCTION(clCreateKernel);
+OPENCL_EXPORTED_FUNCTION(clSetKernelArg);
+OPENCL_EXPORTED_FUNCTION(clEnqueueNDRangeKernel);
+OPENCL_EXPORTED_FUNCTION(clFlush);
+OPENCL_EXPORTED_FUNCTION(clFinish);
+OPENCL_EXPORTED_FUNCTION(clCreateCommandQueue);
+OPENCL_EXPORTED_FUNCTION(clReleaseContext);
+OPENCL_EXPORTED_FUNCTION(clGetPlatformInfo);
+OPENCL_EXPORTED_FUNCTION(clGetExtensionFunctionAddressForPlatform);
+
+#undef OPENCL_EXPORTED_FUNCTION
+
+// Extension functions, loaded using clGetExtensionFunctionAddressForPlatform
+#if !defined(OPENCL_EXPORTED_EXTENSION_FUNCTION)
+#define OPENCL_EXPORTED_EXTENSION_FUNCTION(fun)
+#endif
+
+OPENCL_EXPORTED_EXTENSION_FUNCTION(clImportMemoryARM);
+
+#undef OPENCL_EXPORTED_EXTENSION_FUNCTION