OpenCL compilation debug on Parallella

cldebug.log

coprthr-1.6.2 (Freewill)
[16048] clmesg debug: ocl_platform.c(62): clGetPlatformIDs
[16048] clmesg debug: ocl_device.c(528): __do_discover_devices (nil)
[16048] clmesg debug: device.c(99): __do_discover_devices_1 (nil)
[16048] clmesg debug: device.c(117): h=0x30d7b8 init_device=0xb688a1c0
[16048] clmesg debug: device_x86_64.c(90): init_device_x86_64
[16048] clmesg debug: device.c(128): h=0x2a0020 init_device=0xb684c5d8
[16048] clmesg debug: device_e32.c(113): init_device_e32
[16048] clmesg debug: device_e32.c(128): e_init() returned 0
[16048] clmesg debug: device_e32.c(150): e_alloc using &e_dram 0xb685c364
[16048] clmesg debug: device_e32.c(159): e_alloc ok, returned 0
[16048] clmesg debug: device_e32.c(161): dram alloc:
[16048] clmesg debug: device_e32.c(170): epiphany platform info:
[16048] clmesg debug: device_e32.c(171): 	platform_name 'E16G Needham'
[16048] clmesg debug: device_e32.c(172): 	device_id 9002
[16048] clmesg debug: device_e32.c(173): 	global_mem_base 0x8e100000
[16048] clmesg debug: device_e32.c(174): 	global_mem_size 32505856
[16048] clmesg debug: device_e32.c(175): 	core_local_mem_size 32768
[16048] clmesg debug: device_e32.c(176): 	core_base_addr 0x80800000
[16048] clmesg debug: device_e32.c(177): 	array_ncol 4
[16048] clmesg debug: device_e32.c(178): 	array_nrow 4
[16048] clmesg debug: device_e32.c(192): start set devinfo
[16048] clmesg debug: device.c(138): codevtab[0]=0x3072f0
[16048] clmesg debug: device.c(139): codevtab[1]=0x2a0d80
[16048] clmesg debug: device.c(149): 1 1
[16048] clmesg debug: device.c(149): 2 2
[16048] clmesg debug: device.c(152): navail nall 2 2
[16048] clmesg debug: device.c(161): ndevices 2
[16048] clmesg debug: device.c(168): devtab add 0x3072f0
[16048] clmesg debug: device.c(168): devtab add 0x2a0d80
[16048] clmesg debug: device.c(191): __do_discover_devices_1 ndevices 2
[16048] clmesg debug: ocl_device.c(555): DEVICE 0 is arch x86_64
[16048] clmesg debug: ocl_device.c(561): DEVICE 1 is arch e32
[16048] clmesg debug: ocl_device.c(571): __do_discover_devices ndevices 2
[16048] clmesg debug: ocl_platform.c(74): nplatforms_avail 1

[16048] clmesg debug: ocl_device.c(643): ndevices = 2
[16048] clmesg debug: ocl_device.c(650): match devtype 2 0
[16048] clmesg debug: ocl_device.c(650): match devtype 8 0
[16048] clmesg debug: ocl_device.c(654): n = 1
[16048] clmesg debug: ocl_context.c(51): clCreateContext
[16048] clmesg debug: ocl_context.c(64): clCreateContext: try to get platformid
[16048] clmesg debug: ocl_context.c(304): __find_context_property: (1084) p=1084
[16048] clmesg debug: ocl_context.c(310): __find_context_property: v=30e8b0
[16048] clmesg debug: ocl_context.c(314): __find_context_property: match
[16048] clmesg debug: ocl_command_queue.c(50): clCreateCommandQueue
[16048] clmesg debug: ocl_command_queue.c(55): clCreateCommandQueue 0x30e698
[16048] clmesg debug: ocl_command_queue.c(60): clCreateCommandQueue
[16048] clmesg debug: ocl_command_queue.c(244): __do_create_command_queue: dev=0x2a0d80
[16048] clmesg debug: command_queue.c(67): signaled cmdq1 with qstat ->1

[16048] clmesg debug: ocl_command_queue.c(256): __do_create_command_queue: devnum=0
[16048] clmesg debug: cmdsched.c(57): cmdqx1: cmdq1=0x30e940 dev=0x2a0d80 cpumask_count=?
[16048] clmesg debug: cmdsched.c(73): cmdqx1: idle
[16048] clmesg info: cmdsched.c(86): cmdqx1: run
[16048] clmesg debug: cmdsched.c(90): cmdqx1: queued (nil)
[16048] clmesg debug: cmdsched.c(173): run-cmdqx1 sleep

[16048] clmesg debug: ocl_program.c(54): clCreateProgramWithSource
[16048] clmesg debug: ocl_program.c(516): __do_create_program with ndev = 1
[16048] clmesg debug: ocl_program.c(257): clBuildProgram: progam valid
[16048] clmesg debug: ocl_program.c(263): clBuildProgram: device valid
[16048] clmesg debug: ocl_program.c(286): compiler avail 1
[16048] clmesg debug: ocl_program.c(543): __do_build_program_from_source
[16048] clmesg debug: ocl_program.c(550): __do_build_program_from_source: compiler=0xb448cad4
[16048] clmesg debug: ocl_program.c(555): build_options[0] ||
[16048] clmesg debug: ocl_program.c(557): calling compiler : [0] 0x30ea94 0x30ea90
[16048] clmesg debug: compiler_e32.c(289): __compile_e32
[16048] clmesg debug: compiler_e32.c(298): buf1=0x310930
[16048] clmesg debug: compiler_e32.c(307): opt ||
[16048] clmesg debug: compiler_e32.c(321): opt after filter ||
[16048] clmesg debug: compiler_e32.c(340): wdtemp 0x3149b0|temp/xclXXXXXX|
[16048] clmesg debug: compiler_e32.c(346): wd 0x3149b0|temp/xcl6eUI59|
[16048] clmesg debug: compiler_e32.c(356): compile: work dir temp/xcl6eUI59
[16048] clmesg debug: compiler_e32.c(357): compile: filebase eman39
[16048] clmesg debug: compiler_e32.c(370): PRE log size 24
[16048] clmesg debug: compiler_e32.c(371): ----- log ------
[16048] clmesg debug: compiler_e32.c(372): compiler_e32:build_log:

[16048] clmesg debug: compiler_e32.c(373): ----- log ------
[16048] clmesg debug: compiler_e32.c(385): compile: 0x30eaf0
[16048] clmesg debug: compiler_e32.c(390): wd |temp/xcl6eUI59|
[16048] clmesg debug: compiler_e32.c(394): compile: build from source
[16048] clmesg debug: computil_e32.h(560): execshell> \cp /usr/local/browndeer/lib/_e32pth_core_main_needham.o temp/xcl6eUI59 
[16048] clmesg debug: computil_e32.h(560): execshell> \cp /usr/local/browndeer/lib/_e32pth_core_needham.ldf temp/xcl6eUI59 
[16048] clmesg debug: computil_e32.h(80): trying to write 7702 bytes
[16048] clmesg debug: computil_e32.h(81): last char is (int)10
[16048] clmesg debug: computil_e32.h(98): trying to write 7702 bytes
[16048] clmesg debug: computil_e32.h(560): execshell> cd temp/xcl6eUI59;  e-g++  -O3 -g -Wall -c -fmessage-length=0 -ffast-math -ftree-vectorize -funroll-loops -Wunused-variable -ffp-contract=fast -mlong-calls -mfp-mode=truncate -falign-loops=8 -falign-functions=8 -w -fstack-usage -fno-exceptions -U_FORTIFY_SOURCE -fno-stack-protector -I/opt/adapteva/esdk/tools/e-gnu/epiphany-elf/sys-include -fpermissive -D__coprthr_device__ -x c++ -I/usr/local/browndeer/include -D __xcl_kthr__ --include=e32pth_if_needham.h --include=opencl_lift.h  --include=e32_opencl_ext.h  -D __STDCL_KERNEL_VERSION__=020000 -D__COPRTHR__ -D E32_DRAM_ZEROPAGE=0x8e100000    -S eman39.cpp 
[16048] clmesg debug: computil_e32.h(560): execshell> cd temp/xcl6eUI59;  e-g++  -O3 -g -Wall -c -fmessage-length=0 -ffast-math -ftree-vectorize -funroll-loops -Wunused-variable -ffp-contract=fast -mlong-calls -mfp-mode=truncate -falign-loops=8 -falign-functions=8 -w -fstack-usage -fno-exceptions -U_FORTIFY_SOURCE -fno-stack-protector -I/opt/adapteva/esdk/tools/e-gnu/epiphany-elf/sys-include -fpermissive -D__coprthr_device__ -x c++ -I/usr/local/browndeer/include -D __xcl_kthr__ --include=e32pth_if_needham.h --include=opencl_lift.h  --include=e32_opencl_ext.h  -D __STDCL_KERNEL_VERSION__=020000 -D__COPRTHR__ -D E32_DRAM_ZEROPAGE=0x8e100000    -c eman39.cpp -o e32_eman39.o 
[16048] clmesg debug: compiler_e32.c(429): devmembase = 8e100000
[16048] clmesg debug: computil_e32.h(560): execshell> cd temp/xcl6eUI59; cpp -x c++  -D__coprthr_device__  -I/usr/local/browndeer/include temp/xcl6eUI59/eman39.cl   | awk -v prog=\"temp/xcl6eUI59/eman39.cl\" 'BEGIN { pr=0; } {    if($0~/^#/ && $3==prog) pr=1;   else if ($0~/^#/) pr=0;   if ($0!~/^#/ && pr==1) print $0; }' | xclnm --kcall -d -c -o _kcall_eman39.c - 
cpp: error: temp/xcl6eUI59/eman39.cl: No such file or directory
cpp: warning: ‘-x c++’ after last input file has no effect
cpp: fatal error: no input files
compilation terminated.
[16048] clmesg debug: computil_e32.h(560): execshell> cd temp/xcl6eUI59; cpp -x c++  -D__coprthr_device__  -I/usr/local/browndeer/include temp/xcl6eUI59/eman39.cl   | awk -v prog=\"temp/xcl6eUI59/eman39.cl\" 'BEGIN { pr=0; } {    if($0~/^#/ && $3==prog) pr=1;   else if ($0~/^#/) pr=0;   if ($0!~/^#/ && pr==1) print $0; }' | xclnm --kcall2 -d -c -o _kcall2_eman39.c - 
cpp: error: temp/xcl6eUI59/eman39.cl: No such file or directory
cpp: warning: ‘-x c++’ after last input file has no effect
cpp: fatal error: no input files
compilation terminated.
[16048] clmesg debug: computil_e32.h(560): execshell> cd temp/xcl6eUI59; cpp -x c++  -D__coprthr_device__  -I/usr/local/browndeer/include temp/xcl6eUI59/eman39.cl   | awk -v prog=\"temp/xcl6eUI59/eman39.cl\" 'BEGIN { pr=0; } {    if($0~/^#/ && $3==prog) pr=1;   else if ($0~/^#/) pr=0;   if ($0!~/^#/ && pr==1) print $0; }' | xclnm --kcall3 -d -c -o _kcall3_eman39.c - 
cpp: error: temp/xcl6eUI59/eman39.cl: No such file or directory
cpp: warning: ‘-x c++’ after last input file has no effect
cpp: fatal error: no input files
compilation terminated.
[16048] clmesg debug: computil_e32.h(560): execshell> cd temp/xcl6eUI59; gcc -O0 -fPIC -D__xcl_kcall__ -DE32_DRAM_ZEROPAGE=0x8e100000 -I/usr/local/browndeer/include  --include=sl_engine.h -c _kcall_eman39.c 
[16048] clmesg debug: computil_e32.h(560): execshell> cd temp/xcl6eUI59; gcc -O0 -fPIC -D__xcl_kcall__ -DE32_DRAM_ZEROPAGE=0x8e100000 -I/usr/local/browndeer/include  --include=sl_engine.h -c _kcall2_eman39.c 
[16048] clmesg debug: compiler_e32.c(459): compile kcall wrapper
[16048] clmesg debug: computil_e32.h(560): execshell> cd temp/xcl6eUI59;  e-gcc  -O0 -g -Wall -c -fmessage-length=0 -ffast-math -ftree-vectorize -funroll-loops -Wunused-variable -ffp-contract=fast -mlong-calls -mfp-mode=round-nearest -w -fstack-usage -fno-exceptions -U_FORTIFY_SOURCE -fno-stack-protector -I/opt/adapteva/esdk/tools/e-gnu/epiphany-elf/sys-include -fpermissive -D__coprthr_device__  -DE32_DRAM_ZEROPAGE=0x8e100000 -I/usr/local/browndeer/include -D__xcl_kcall__ --include=e32pth_if_needham.h -c _kcall3_eman39.c -o e32_kcall3_eman39.o 
[16048] clmesg debug: compiler_e32.c(466): link core prog for all cores
[16048] clmesg debug: computil_e32.h(560): execshell> cd temp/xcl6eUI59; e-ld -r -o e32.o _e32pth_core_main_needham.o e32_eman39.o e32_kcall3_eman39.o -L/opt/adapteva/esdk/tools/e-gnu/epiphany-elf/lib -le-lib 
[16048] clmesg debug: computil_e32.h(560): execshell> cd temp/xcl6eUI59;  e-gcc  -o e32.0.elf  e32.o  -T _e32pth_core_needham.ldf -lm;  e-objcopy  --srec-forceS3 --output-target srec e32.0.elf e32.0.srec 
[16048] clmesg debug: computil_e32.h(560): execshell> cd temp/xcl6eUI59; cat e32.0.srec > e32.srec
[16048] clmesg debug: compiler_e32.c(491): extract sym and arg data
[16048] clmesg debug: computil_e32.h(262): cd temp/xcl6eUI59;cpp -x c++ -I/usr/local/browndeer/include temp/xcl6eUI59/eman39.cl   | awk -v prog=\"temp/xcl6eUI59/eman39.cl\" 'BEGIN { pr=0; } {    if($0~/^#/ && $3==prog) pr=1;   else if ($0~/^#/) pr=0;   if ($0!~/^#/ && pr==1) print $0; }' | xclnm -n -d - 
cpp: error: temp/xcl6eUI59/eman39.cl: No such file or directory
cpp: warning: ‘-x c++’ after last input file has no effect
cpp: fatal error: no input files
compilation terminated.
cpp: error: temp/xcl6eUI59/eman39.cl: No such file or directory
cpp: warning: ‘-x c++’ after last input file has no effect
cpp: fatal error: no input files
compilation terminated.
[16048] clmesg debug: compiler_e32.c(500): narg 1
[16048] clmesg debug: computil_e32.h(360): > cd temp/xcl6eUI59; nm --defined-only e32.0.elf
[16048] clmesg debug: computil_e32.h(401): addr_core_local_data = 0x2b68
[16048] clmesg debug: computil_e32.h(426): execshell> cd temp/xcl6eUI59; sed 's/(.*)//' eman39.su |awk '{print $2 " " $3}'
[16048] clmesg debug: computil_e32.h(433): stack usage: 'setup_ctx' 16

[16048] clmesg debug: computil_e32.h(433): stack usage: 'sha512' 280

[16048] clmesg debug: computil_e32.h(433): stack usage: 'bitmessage_pow' 72

[16048] clmesg debug: computil_e32.h(452): execshell> cd temp/xcl6eUI59; awk -F: '{print $4}' e32_kcall3_eman39.su | awk '{print $1 " " $2}'
[16048] clmesg debug: computil_e32.h(458): stack usage: 'barrier' 16

[16048] clmesg debug: compiler_e32.c(513): A
[16048] clmesg debug: compiler_e32.c(515): B
[16048] clmesg debug: compiler_e32.c(520): C
[16048] clmesg debug: computil_e32.h(485): build_clargtab
[16048] clmesg debug: computil_e32.h(487): p_clargtab=0xbeea6618
[16048] clmesg debug: computil_e32.h(492): *p_clargtab=0x314980
[16048] clmesg debug: computil_e32.h(520): cmd=cd temp/xcl6eUI59;cpp -x c++ -I/usr/local/browndeer/include temp/xcl6eUI59/eman39.cl   | awk -v prog=\"temp/xcl6eUI59/eman39.cl\" 'BEGIN { pr=0; } {    if($0~/^#/ && $3==prog) pr=1;   else if ($0~/^#/) pr=0;   if ($0!~/^#/ && pr==1) print $0; }' | xclnm --clargtab -d -c - 
[16048] clmesg debug: computil_e32.h(523): fp=0x315100
cpp: error: temp/xcl6eUI59/eman39.cl: No such file or directory
cpp: warning: ‘-x c++’ after last input file has no effect
cpp: fatal error: no input files
compilation terminated.
[16048] clmesg debug: computil_e32.h(531): 0 (null) 0 0 0 0 0 0 () 
[16048] clmesg debug: computil_e32.h(544): after pclose
[16048] clmesg debug: compiler_e32.c(523): D
[16048] clmesg debug: compiler_e32.c(527): i=0 narg=1

[16048] clmesg debug: compiler_e32.c(531): wd |temp/xcl6eUI59|
[16048] clmesg debug: compiler_e32.c(533): /* now build elf/cl object */
[16048] clmesg debug: compiler_e32.c(551): wd |temp/xcl6eUI59|
[16048] clmesg debug: compiler_e32.c(553): SHELLCMD_OBJCOPY_STEP
[16048] clmesg debug: computil_e32.h(560): execshell> cd temp/xcl6eUI59;  objcopy -I binary -O elf32-littlearm -B arm e32.srec data_srec_e32.o 
[16048] clmesg debug: compiler_e32.c(560): SHELLCMD_GEN_PROGINFO_OBJ
[16048] clmesg debug: computil_e32.h(560): execshell> cd temp/xcl6eUI59;echo 'struct _program_info_struct {unsigned int core_local_data;unsigned int stack_size;} _program_info = (struct _program_info_struct){ 0x2b68, 0x100 };' > _program_info.c;gcc -c _program_info.c
[16048] clmesg debug: compiler_e32.c(567): SHELLCMD_CXXLINK_LIB
[16048] clmesg debug: computil_e32.h(560): execshell> cd temp/xcl6eUI59; g++ -shared -Wl,-soname,data_srec_e32.so -o data_srec_e32.so data_srec_e32.o eman39.elfcl _program_info.o 
[16048] clmesg debug: compiler_e32.c(580): wd |temp/xcl6eUI59|
[16048] clmesg debug: compiler_e32.c(588): copy_file_to_mem
[16048] clmesg debug: compiler_e32.c(590): wd 0x3149b0|temp/xcl6eUI59|
[16048] clmesg debug: computil_e32.h(214): path=temp/xcl6eUI59//data_srec_e32.so
[16048] clmesg debug: computil_e32.h(222): fd=6
[16048] clmesg debug: computil_e32.h(226): p_sz=0x30ea90
[16048] clmesg debug: computil_e32.h(227): p_buf=0x30ea94
[16048] clmesg debug: computil_e32.h(231): *p_buf=0x317b88
[16048] clmesg debug: computil_e32.h(234): n=47471
[16048] clmesg debug: computil_e32.h(238): returning
[16048] clmesg debug: compiler_e32.c(593): wd 0x3149b0|temp/xcl6eUI59|
[16048] clmesg debug: compiler_e32.c(594): back from copy_file_to_mem
[16048] clmesg debug: compiler_e32.c(596): after check err
[16048] clmesg debug: compiler_e32.c(598): wd |temp/xcl6eUI59|
[16048] clmesg debug: compiler_e32.c(599): conditional remove work dir: before |temp/xcl6eUI59|
[16048] clmesg debug: compiler_e32.c(601): conditional remove work dir: after
[16048] clmesg debug: compiler_e32.c(605): log size 4367
[16048] clmesg debug: compiler_e32.c(606): ----- log ------
[16048] clmesg debug: compiler_e32.c(607): compiler_e32:build_log:
execshell> \cp /usr/local/browndeer/lib/_e32pth_core_main_needham.o temp/xcl6eUI59 

execshell> \cp /usr/local/browndeer/lib/_e32pth_core_needham.ldf temp/xcl6eUI59 

execshell> cd temp/xcl6eUI59;  e-g++  -O3 -g -Wall -c -fmessage-length=0 -ffast-math -ftree-vectorize -funroll-loops -Wunused-variable -ffp-contract=fast -mlong-calls -mfp-mode=truncate -falign-loops=8 -falign-functions=8 -w -fstack-usage -fno-exceptions -U_FORTIFY_SOURCE -fno-stack-protector -I/opt/adapteva/esdk/tools/e-gnu/epiphany-elf/sys-include -fpermissive -D__coprthr_device__ -x c++ -I/usr/local/browndeer/include -D __xcl_kthr__ --include=e32pth_if_needham.h --include=opencl_lift.h  --include=e32_opencl_ext.h  -D __STDCL_KERNEL_VERSION__=020000 -D__COPRTHR__ -D E32_DRAM_ZEROPAGE=0x8e100000    -S eman39.cpp 

execshell> cd temp/xcl6eUI59;  e-g++  -O3 -g -Wall -c -fmessage-length=0 -ffast-math -ftree-vectorize -funroll-loops -Wunused-variable -ffp-contract=fast -mlong-calls -mfp-mode=truncate -falign-loops=8 -fal
[16048] clmesg debug: compiler_e32.c(608): ----- log ------
[16048] clmesg debug: ocl_program.c(533): __do_build_program_from_binary
[16048] clmesg debug: program.c(59): __do_build_program_from_binary_1
[16048] clmesg debug: program.c(66): program: bin bin_sz 0x317b88 47471
[16048] clmesg debug: program.c(86): is this elf? |E L F 
[16048] clmesg debug: program.c(108): section name ||
[16048] clmesg debug: program.c(108): section name |.note.gnu.build-id|
[16048] clmesg debug: program.c(108): section name |.gnu.hash|
[16048] clmesg debug: program.c(108): section name |.dynsym|
[16048] clmesg debug: program.c(108): section name |.dynstr|
[16048] clmesg debug: program.c(108): section name |.rel.dyn|
[16048] clmesg debug: program.c(108): section name |.rel.plt|
[16048] clmesg debug: program.c(108): section name |.init|
[16048] clmesg debug: program.c(108): section name |.plt|
[16048] clmesg debug: program.c(108): section name |.text|
[16048] clmesg debug: program.c(108): section name |.fini|
[16048] clmesg debug: program.c(108): section name |.clargtab|
[16048] clmesg debug: program.c(108): section name |.clstrtab|
[16048] clmesg debug: program.c(108): section name |.eh_frame|
[16048] clmesg debug: program.c(108): section name |.init_array|
[16048] clmesg debug: program.c(108): section name |.fini_array|
[16048] clmesg debug: program.c(108): section name |.jcr|
[16048] clmesg debug: program.c(108): section name |.dynamic|
[16048] clmesg debug: program.c(108): section name |.got|
[16048] clmesg debug: program.c(108): section name |.data|
[16048] clmesg debug: program.c(108): section name |.bss|
[16048] clmesg debug: program.c(108): section name |.comment|
[16048] clmesg debug: program.c(108): section name |.ARM.attributes|
[16048] clmesg debug: program.c(108): section name |.shstrtab|
[16048] clmesg debug: program.c(108): section name |.symtab|
[16048] clmesg debug: program.c(108): section name |.strtab|
[16048] clmesg debug: program.c(124): clstrtab_sz 8

[16048] clmesg debug: program.c(137): [0] clarg |(null)| (+1)
[16048] clmesg debug: program.c(298): _program_info found
[16048] clmesg debug: program.c(306): srec srec_end srec_sz 0xb3c2c02c 0xb3c35be4 39864
[16048] clmesg debug: program.c(447): prg1->v_ksyms=0x3156d8
[16048] clmesg debug: program.c(456): kbin = 0x315418
[16048] clmesg debug: program.c(478): build_log=0x316a70
[16048] clmesg debug: ocl_memobj.c(62): clCreateBuffer
[16048] clmesg debug: ocl_memobj.c(96): malloc returned 0x315758
[16048] clmesg debug: ocl_memobj.c(450): using static resource allocation across devices
[16048] clmesg debug: ocl_memobj.c(459): XXX memalloc 0xb684e78c
[16048] clmesg debug: devops_e32.c(51): arch/e32: memalloc 88 0x1
[16048] clmesg debug: devops_e32.c(71): memalloc type=BUFFER res=0x8e104000
[16048] clmesg debug: ocl_memobj.c(474): __do_create_buffer: mem1[0]=0x3157b8 (88)
[16048] clmesg debug: ocl_memobj.c(482): malloc'd 88 bytes
[16048] clmesg debug: ocl_memobj.c(487): CL_MEM_COPY_HOST_PTR
[16048] clmesg debug: devops_e32.c(194): xxx_e_write_dram &e_dram=0xb685c364 dst=0x8e104000 (dst-devmembase=0x4000)
[16048] clmesg debug: ocl_memobj.c(503): past
[16048] clmesg debug: ocl_memobj.c(517): __do_create_buffer return
[16048] clmesg debug: ocl_memobj.c(62): clCreateBuffer
[16048] clmesg debug: ocl_memobj.c(96): malloc returned 0x315808
[16048] clmesg debug: ocl_memobj.c(450): using static resource allocation across devices
[16048] clmesg debug: ocl_memobj.c(459): XXX memalloc 0xb684e78c
[16048] clmesg debug: devops_e32.c(51): arch/e32: memalloc 8 0x1
[16048] clmesg debug: devops_e32.c(71): memalloc type=BUFFER res=0x8e105000
[16048] clmesg debug: ocl_memobj.c(474): __do_create_buffer: mem1[0]=0x315868 (8)
[16048] clmesg debug: ocl_memobj.c(482): malloc'd 8 bytes
[16048] clmesg debug: ocl_memobj.c(503): past
[16048] clmesg debug: ocl_memobj.c(517): __do_create_buffer return
[16048] clmesg debug: ocl_kernel.c(47): clCreateKernel
[16048] clmesg debug: ocl_program.c(574): nkrn 0
[16048] clmesg debug: ocl_kernel.c(164): clSetKernelArg
[16048] clmesg debug: ocl_kernel.c(164): clSetKernelArg
[16048] clmesg debug: ocl_kernel.c(164): clSetKernelArg
[16048] clmesg debug: ocl_enqueue.c(870): clEnqueueNDRangeKernel gwo=(nil)
[16048] clmesg debug: ocl_enqueue.c(103): clEnqueueReadBuffer
[16048] clmesg debug: ocl_enqueue.c(107): clEnqueueReadBuffer: membuf=0x315808
[16048] clmesg debug: ocl_enqueue.c(108): clEnqueueReadBuffer: membuf->type=4336
[16048] clmesg debug: ocl_enqueue.c(109): clEnqueueReadBuffer: __invalid_membuf()=0
[16048] clmesg debug: ocl_enqueue.c(112): clEnqueueReadBuffer: membuf->sz=8
[16048] clmesg debug: ocl_enqueue.c(131): test lock
[16048] clmesg debug: ocl_enqueue.c(132): __lock_event: attempt 0x3158c0
[16048] clmesg debug: ocl_enqueue.c(132): __lock_event: locked 0x3158c0
[16048] clmesg debug: ocl_enqueue.c(133): __unlock_event: unlocked 0x3158c0
[16048] clmesg debug: event.c(65): __do_set_cmd_read_buffer_1: src1=0x315868
[16048] clmesg debug: command_queue.c(115): __do_enqueue_cmd_1: ev 0x3158e0
[16048] clmesg debug: command_queue.c(117): cmdq1 0x30e940
[16048] clmesg debug: ocl_enqueue.c(166): blocking on event 0x3158c0
[16048] clmesg debug: ocl_enqueue.c(166): __lock_event: attempt 0x3158c0
[16048] clmesg debug: ocl_enqueue.c(166): __lock_event: locked 0x3158c0
[16048] clmesg debug: cmdsched.c(175): run-cmdqx1 wake

[16048] clmesg debug: cmdsched.c(90): cmdqx1: queued 0x3158e0
[16048] clmesg debug: cmdsched.c(95): cmdqx1: submit cmd ev1 0x3158e0
[16048] clmesg debug: cmdsched.c(101): cmdqx1: attempt __lock_event1
[16048] clmesg debug: cmdsched.c(102): __lock_event1: attempt 0x3158e0
[16048] clmesg debug: ocl_enqueue.c(166): wait-sleep on event 0x3158c0

[16048] clmesg debug: ocl_enqueue.c(166): __wait_event: sleep0x3158c0
[16048] clmesg debug: cmdsched.c(102): __lock_event1: locked 0x3158e0
[16048] clmesg debug: cmdsched.c(112): 0x3158e0: XXX submit 4

[16048] clmesg debug: devcmds_e32.c(169): cmdcall_e32:read_buffer
[16048] clmesg debug: devcmds_e32.c(175): cmdcall_e32:read_buffer m.src 0x315868
[16048] clmesg debug: devcmds_e32.c(179): 0xbeea6fc8 0x8e105000 0
[16048] clmesg debug: devcmds_e32.c(181): xxx_e_read_dram &e_dram=0xb685c364 src=0x8e105000 (src-devmembase=0x5000)
[16048] clmesg debug: cmdsched.c(114): 0x3158e0: XXX submitted 4

[16048] clmesg debug: cmdsched.c(117): __sig_event1: attempt signal 0x3158e0
[16048] clmesg debug: cmdsched.c(117): __sig_event1: signaled 0x3158e0
[16048] clmesg debug: cmdsched.c(119): __unlock_event1: attempt unlock 0x3158e0
[16048] clmesg debug: cmdsched.c(119): __unlock_event1: unlocked 0x3158e0
[16048] clmesg debug: cmdsched.c(132): __lock_event1: attempt 0x3158e0
[16048] clmesg debug: cmdsched.c(132): __lock_event1: locked 0x3158e0
[16048] clmesg debug: cmdsched.c(140): 0x3158e0: running 4

[16048] clmesg debug: cmdsched.c(143): __sig_event1: attempt signal 0x3158e0
[16048] clmesg debug: cmdsched.c(143): __sig_event1: signaled 0x3158e0
[16048] clmesg debug: cmdsched.c(145): __unlock_event1: attempt unlock 0x3158e0
[16048] clmesg debug: cmdsched.c(145): __unlock_event1: unlocked 0x3158e0
[16048] clmesg debug: cmdsched.c(153): __lock_event1: attempt 0x3158e0
[16048] clmesg debug: cmdsched.c(153): __lock_event1: locked 0x3158e0
[16048] clmesg debug: cmdsched.c(162): __sig_event1: attempt signal 0x3158e0
[16048] clmesg debug: cmdsched.c(162): __sig_event1: signaled 0x3158e0
[16048] clmesg debug: cmdsched.c(164): __unlock_event1: attempt unlock 0x3158e0
[16048] clmesg debug: cmdsched.c(164): __unlock_event1: unlocked 0x3158e0
[16048] clmesg debug: cmdsched.c(166): 0x3158e0: complete 4

[16048] clmesg debug: cmdsched.c(173): run-cmdqx1 sleep

[16048] clmesg debug: ocl_enqueue.c(166): __wait_event: wake0x3158c0
[16048] clmesg debug: ocl_enqueue.c(166): wait-wake on event 0x3158c0
[16048] clmesg debug: ocl_enqueue.c(166): event 0x3158c0 complete

[16048] clmesg debug: ocl_enqueue.c(166): __unlock_event: unlocked 0x3158c0
[16048] clmesg debug: ocl_kernel.c(146): clReleaseKernel
[16048] clmesg debug: ocl_program.c(234): clReleaseProgram
[16048] clmesg debug: ocl_memobj.c(248): clReleaseMemObject
[16048] clmesg debug: ocl_memobj.c(248): clReleaseMemObject
[16048] clmesg debug: ocl_command_queue.c(112): clReleaseCommandQueue
[16048] clmesg debug: cmdsched.c(175): run-cmdqx1 wake

[16048] clmesg info: cmdsched.c(181): cmdqx1: shutdown
[16048] clmesg debug: command_queue.c(103): __do_release_command_queue_1: cmdq->td joinied with status 0
[16048] clmesg debug: ocl_command_queue.c(121): before __coprthr_free_command_queue
[16048] clmesg debug: ocl_command_queue.c(121): after __coprthr_free_command_queue
[16048] clmesg debug: ocl_context.c(230): clReleaseContext

 Error number -46
 Error number -48
 Error number -48
 Error number -48
 Error number -48C
===========
Nonce: 4939586775259335885; time: 12.424335; speed: 397573534044816256.00 hash/s
Traceback (most recent call last):
  File "./testcl.py", line 93, in <module>
    assert result <= target, "nonce gives not good enough trial value!"
AssertionError: nonce gives not good enough trial value!