IMX6 Opencl CL_OUT_OF_RESOURCES CrateKernel Why???

[weikangyang]

 ./clinfo

>>>>>>>> ./clinfo Starting...

Available platforms: 1

Platform ID: 0
CL_PLATFORM_NAME: Vivante OpenCL Platform
CL_PLATFORM_PROFILE: EMBEDDED_PROFILE
CL_PLATFORM_VERSION: OpenCL 1.1
CL_PLATFORM_VENDOR: Vivante Corporation
CL_PLATFORM_EXTENSIONS: None

Available devices: 1

Device ID: 0
Device Ptr: 0x2ab202c8
CL_DEVICE_NAME: Vivante OpenCL Device
CL_DEVICE_VENDOR: Vivante Corporation
CL_DEVICE_TYPE: GPU
CL_DEVICE_OPENCL_C_VERSION: OpenCL C 1.1
CL_DEVICE_VENDOR_ID: 0x00564956
CL_DEVICE_PLATFORM: 0x2ab20448
CL_DEVICE_VERSION: OpenCL 1.1
CL_DEVICE_PROFILE: EMBEDDED_PROFILE
CL_DRIVER_VERSION: OpenCL 1.1
CL_DEVICE_MAX_COMPUTE_UNITS: 1
CL_DEVICE_MAX_WORK_ITEM_DIMENSIONS: 3
CL_DEVICE_MAX_WORK_ITEM_SIZES[0]: 256
CL_DEVICE_MAX_WORK_ITEM_SIZES[1]: 256
CL_DEVICE_MAX_WORK_ITEM_SIZES[2]: 256
CL_DEVICE_MAX_WORK_GROUP_SIZE: 256
CL_DEVICE_MAX_CLOCK_FREQUENCY: 500 MHz
CL_DEVICE_IMAGE_SUPPORT: Yes
CL_DEVICE_MAX_READ_IMAGE_ARGS: 8
CL_DEVICE_MAX_WRITE_IMAGE_ARGS: 8
CL_DEVICE_IMAGE2D_MAX_WIDTH: 8192
CL_DEVICE_IMAGE2D_MAX_HEIGHT: 8192
CL_DEVICE_IMAGE3D_MAX_WIDTH: 0
CL_DEVICE_IMAGE3D_MAX_HEIGHT: 0
CL_DEVICE_IMAGE3D_MAX_DEPTH: 0
CL_DEVICE_MAX_SAMPLERS: 8

CL_DEVICE_EXTENSIONS: cl_khr_byte_addressable_store

CL_DEVICE_PREFERRED_VECTOR_WIDTH_CHAR: 4
CL_DEVICE_PREFERRED_VECTOR_WIDTH_SHORT: 4
CL_DEVICE_PREFERRED_VECTOR_WIDTH_INT: 4
CL_DEVICE_PREFERRED_VECTOR_WIDTH_LONG: 0
CL_DEVICE_PREFERRED_VECTOR_WIDTH_FLOAT: 4
CL_DEVICE_PREFERRED_VECTOR_WIDTH_DOUBLE: 0
CL_DEVICE_NATIVE_VECTOR_WIDTH_CHAR: 4
CL_DEVICE_NATIVE_VECTOR_WIDTH_SHORT: 4
CL_DEVICE_NATIVE_VECTOR_WIDTH_INT: 4
CL_DEVICE_NATIVE_VECTOR_WIDTH_LONG: 0
CL_DEVICE_NATIVE_VECTOR_WIDTH_FLOAT: 4
CL_DEVICE_NATIVE_VECTOR_WIDTH_DOUBLE: 0
CL_DEVICE_MAX_PARAMETER_SIZE: 256
CL_DEVICE_MEM_BASE_ADDR_ALIGN: 1024
CL_DEVICE_MIN_DATA_TYPE_ALIGN_SIZE: 128
CL_DEVICE_SINGLE_FP_CONFIG:
CL_FP_DENORM: No
CL_FP_INF_NAN: No
CL_FP_ROUND_TO_NEAREST: No
CL_FP_ROUND_TO_ZERO: Yes
CL_FP_ROUND_TO_INF: No
CL_FP_FMA: No
CL_FP_SOFT_FLOAT: No
CL_DEVICE_ADDRESS_BITS: 32
CL_DEVICE_GLOBAL_MEM_SIZE: 64 MByte
CL_DEVICE_MAX_MEM_ALLOC_SIZE: 32 MByte
CL_DEVICE_GLOBAL_MEM_CACHE_TYPE: Read/Write
CL_DEVICE_GLOBAL_MEM_CACHELINE_SIZE: 64
CL_DEVICE_GLOBAL_MEM_CACHE_SIZE: 8192
CL_DEVICE_LOCAL_MEM_SIZE: 1 KByte
CL_DEVICE_LOCAL_MEM_TYPE: Global
CL_DEVICE_MAX_CONSTANT_BUFFER_SIZE: 4 KByte
CL_DEVICE_MAX_CONSTANT_ARGS: 9
CL_DEVICE_ERROR_CORRECTION_SUPPORT: Yes
CL_DEVICE_QUEUE_PROPERTIES:
CL_QUEUE_OUT_OF_ORDER_EXEC_MODE_ENABLE:Yes
CL_QUEUE_PROFILING_ENABLE: Yes
CL_DEVICE_HOST_UNIFIED_MEMORY: Yes
CL_DEVICE_PROFILING_TIMER_RESOLUTION: 1000
CL_DEVICE_ENDIAN_LITTLE: Yes
CL_DEVICE_AVAILABLE: Yes
CL_DEVICE_COMPILER_AVAILABLE: Yes
CL_DEVICE_EXECUTION_CAPABILITIES:
CL_EXEC_KERNEL: Yes
CL_EXEC_NATIVE_KERNEL: No

>>>>>>>> Creating CLInfo context...

Context Properties:
Context Ptr: 0x33274e50
CL_CONTEXT_REFERENCE_COUNT: 1
CL_CONTEXT_NUM_DEVICES: 1
CL_CONTEXT_DEVICES: 0x2ab202c8
CL_CONTEXT_PROPERTIES: 0x00001084
0x2ab20448
0x00000000

>>>>>>>> Creating CLInfo command queue...

Command Queue Properties:
CL_QUEUE_CONTEXT: 0x33274e50
CL_QUEUE_DEVICE: 0x2ab202c8
CL_QUEUE_REFERENCE_COUNT: 1
CL_QUEUE_PROPERTIES:
CL_QUEUE_OUT_OF_ORDER_EXEC_MODE_ENABLE:Yes
CL_QUEUE_PROFILING_ENABLE: Yes

>>>>>>>> Creating CLInfo program...

>>>>>>>> Building CLInfo program...

Program Properties:
CL_PROGRAM_CONTEXT: 0x33274e50
CL_PROGRAM_REFERENCE_COUNT: 1
CL_PROGRAM_NUM_DEVICES: 1
CL_PROGRAM_DEVICES: 0x2ab202c8
CL_PROGRAM_SOURCE: (Size:60)

------------------ BEGIN --------------------
__kernel void hello() { size_t i = get_global_id(0); }
------------------- END ---------------------

CL_PROGRAM_BINARY_SIZES[0]: 232
CL_PROGRAM_BINARIES:
Device Number 0:

------------------ BEGIN --------------------
SHDR CL #global_id i hello k 0 0
------------------- END ---------------------

Program Build Properties:
CL_PROGRAM_BUILD_STATUS: 0
CL_PROGRAM_BUILD_OPTIONS: ""
CL_PROGRAM_BUILD_LOG: ""

>>>>>>>> Creating CLInfo kernel...

Kernel Properties:
CL_KERNEL_FUNCTION_NAME: "hello"
CL_KERNEL_CONTEXT: 0x33274e50
CL_KERNEL_PROGRAM: 0x332736a0
CL_KERNEL_NUM_ARGS: 0
CL_KERNEL_REFERENCE_COUNT: 1

Kernel Workgroup Properties:
CL_KERNEL_WORK_GROUP_SIZE: 48
CL_KERNEL_PREFERRED_WORK_GROUP_SIZE_MULTIPLE: 4
CL_KERNEL_COMPILE_WORK_GROUP_SIZE: 0
0
0
CL_KERNEL_LOCAL_MEM_SIZE: 0
CL_KERNEL_PRIVATE_MEM_SIZE: 0

>>>>>>>> Releasing CLInfo kernel...

>>>>>>>> Releasing CLInfo program...

>>>>>>>> Releasing CLInfo command queue...

>>>>>>>> Releasing CLInfo context...

>>>>>>>> Press <Enter> to quit...

>>>>>>>> Exiting...

 /mnt/functions_and_kernels
TESTS STARTED...
ERROR: Unable to create kernel! (CL_OUT_OF_RESOURCES from main.cpp:212)
ERROR: Unable to create kernel! (CL_OUT_OF_RESOURCES from main.cpp:212)
ERROR: Unable to create kernel! (CL_OUT_OF_RESOURCES from main.cpp:212)
Total Tests: 72
Passed: 0
Failed:2
TESTS ENDED

 cat /proc/cpuinfo
Processor : ARMv7 Processor rev 10 (v7l)
processor : 0
BogoMIPS : 790.52

processor : 1
BogoMIPS : 790.52

Features : swp half thumb fastmult vfp edsp neon vfpv3
CPU implementer : 0x41
CPU architecture: 7
CPU variant : 0x2
CPU part : 0xc09
CPU revision : 10

Hardware : Freescale i.MX 6Quad/DualLite/Solo Sabre-SD Board
Revision : 61011
Serial : 0000000000000000
[root@medcaptain work]#

 uname -a
Linux 3.0.35-2666-gbdde708+ #3 SMP PREEMPT Tue Dec 18 20:03:30 CST 2018 armv7l GNU/Linux

[weikangyang]

Under bsp version 3.0.35， GPU OpenCL can not work？。。。can give me an link to download bsp 3.0.35 ?it can download from nxp website ? because our product use Linux 3.0.35..thanks?

[igorpadykov]

i.MX 6Quad, i.MX 6Dual, i.MX 6DualLite, i.MX 6Solo and i.MX 6Sololite Linux BSP Source Code Files

https://www.nxp.com/webapp/Download?colCode=L3.0.35_4.1.0_ER_SOURCE_BSP&amp;appType=license&amp;loca...

[weikangyang]

hi igorpadykow

i Use 3.0.35 BSP to build，ltlib tool compiler kernel，but the gpu opencl also can not work，Can you ensure that under nxp 3.0.35 BSP， the opencl can work well？ our product use 3.0.35，can not use other bsp to solve this problem？

Thanks

[igorpadykov]

Hi wei

one can try to follow

OpenCL Hello World 

White Paper on get started with OpenCL on iMX6.pdf 

reason for Opencl CL_OUT_OF_RESOURCES may be that Linux 3.0.35

is very old kernel, one can try with latest yocto versions.

i.MX Software|NXP 

Best regards
igor
-----------------------------------------------------------------------------------------------------------------------
Note: If this post answers your question, please click the Correct Answer button. Thank you!
-----------------------------------------------------------------------------------------------------------------------