AnsweredAssumed Answered

IMX6 Opencl CL_OUT_OF_RESOURCES CrateKernel Why???

Question asked by weikang yang on Dec 18, 2018
Latest reply on Jan 28, 2019 by weikang yang

 ./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

Outcomes