Got CL_INVALID_BINARY error when emulated HelloWorld example on Windows

You should run your host code using the following command:

env CL_CONTEXT_EMULATOR_DEVICE_ALTERA=1 host.exe

Or run "set CL_CONTEXT_EMULATOR_DEVICE_ALTERA=1" in the same command window right before running your host code. The way it is, the host code is trying to use your integrated GPU (iGPU) which obviously wouldn't work using the FPGA emulator binary.

--- Quote Start ---

You should run your host code using the following command:

env CL_CONTEXT_EMULATOR_DEVICE_ALTERA=1 host.exe

Or run "set CL_CONTEXT_EMULATOR_DEVICE_ALTERA=1" in the same command window right before running your host code. The way it is, the host code is trying to use your integrated GPU (iGPU) which obviously wouldn't work using the FPGA emulator binary.

--- Quote End ---

Hi,

Thanks for the reply.

I tried "env CL_CONTEXT_EMULATOR_DEVICE_ALTERA=1 host.exe", but the command window showed "'env' is not an internal or external command". So I tried to run "set CL_CONTEXT_EMULATOR_DEVICE_ALTERA=1", and execute host.exe right away (in the same command window). However, I still got the same error message about CL_INVALID_BINARY.

Commands and results are as following:

C:\Users\1705061\exm_opencl_hello_world_x64_windows\hello_world\bin>set CL_CONTEXT_EMULATOR_DEVICE_ALTERA=1

C:\Users\1705061\exm_opencl_hello_world_x64_windows\hello_world\bin>host.exe

Querying platform for info:

==========================

CL_PLATFORM_NAME = Intel(R) OpenCL

CL_PLATFORM_VENDOR = Intel(R) Corporation

CL_PLATFORM_VERSION = OpenCL 2.0

Querying device for info:

========================

CL_DEVICE_NAME = Intel(R) HD Graphics 520

CL_DEVICE_VENDOR = Intel(R) Corporation

CL_DEVICE_VENDOR_ID = 32902

CL_DEVICE_VERSION = OpenCL 2.0

CL_DRIVER_VERSION = 20.19.15.4331

CL_DEVICE_ADDRESS_BITS = 64

CL_DEVICE_AVAILABLE = true

CL_DEVICE_ENDIAN_LITTLE = true

CL_DEVICE_GLOBAL_MEM_CACHE_SIZE = 524288

CL_DEVICE_GLOBAL_MEM_CACHELINE_SIZE = 64

CL_DEVICE_GLOBAL_MEM_SIZE = 1360632218

CL_DEVICE_IMAGE_SUPPORT = true

CL_DEVICE_LOCAL_MEM_SIZE = 65536

CL_DEVICE_MAX_CLOCK_FREQUENCY = 1000

CL_DEVICE_MAX_COMPUTE_UNITS = 24

CL_DEVICE_MAX_CONSTANT_ARGS = 8

CL_DEVICE_MAX_CONSTANT_BUFFER_SIZE = 65536

CL_DEVICE_MAX_WORK_ITEM_DIMENSIONS = 3

CL_DEVICE_MEM_BASE_ADDR_ALIGN = 1024

CL_DEVICE_MIN_DATA_TYPE_ALIGN_SIZE = 128

CL_DEVICE_PREFERRED_VECTOR_WIDTH_CHAR = 1

CL_DEVICE_PREFERRED_VECTOR_WIDTH_SHORT = 1

CL_DEVICE_PREFERRED_VECTOR_WIDTH_INT = 1

CL_DEVICE_PREFERRED_VECTOR_WIDTH_LONG = 1

CL_DEVICE_PREFERRED_VECTOR_WIDTH_FLOAT = 1

CL_DEVICE_PREFERRED_VECTOR_WIDTH_DOUBLE = 0

Command queue out of order? = false

Command queue profiling enabled? = true

Using AOCX: hello_world.aocx

Context callback: Invalid binary.

ERROR: CL_INVALID_BINARY

Location: ..\common\src\AOCLUtils\opencl.cpp:392

Failed to create program with binary

C:\Users\1705061\exm_opencl_hello_world_x64_windows\hello_world\bin>

It is still trying to use your GPU. The GPU should not be detected at all if the host code is compiled correctly; you probably have made some mistake in compiling your host code.

Still, try this:

host\src\main.cpp, line 136, change:

devices.reset(getDevices(platform, CL_DEVICE_TYPE_ALL, &num_devices));

with:

devices.reset(getDevices(platform, CL_DEVICE_TYPE_ACCELERATOR, &num_devices));

And see if it detects Altera's emulated device instead. If it doesn't find anything, then you have made some mistake in compiling/linking the host code.

This is the result after I modified main.cpp and re-complied.

C:\Users\1705061\exm_opencl_hello_world_x64_windows\hello_world\bin>host.exe

Querying platform for info:

==========================

CL_PLATFORM_NAME = Intel(R) OpenCL

CL_PLATFORM_VENDOR = Intel(R) Corporation

CL_PLATFORM_VERSION = OpenCL 2.0

ERROR: CL_DEVICE_NOT_FOUND

Location: ..\common\src\AOCLUtils\opencl.cpp:356

Query for number of devices failed

The instruction mentioned "Link your host application to the libraries returned by the aocl linkflags utility command.", but didn't point out how to link...

May I ask how to link the host.exe with libraries?

This is the result after run "aocl linkflages".

C:\Users\1705061\exm_opencl_hello_world_x64_windows\hello_world\bin>aocl linkflags

/libpath:C:\intelFPGA\17.0\hld\board\s5_ref/windows64/lib /libpath:C:/intelFPGA/17.0/hld/host/windows64/lib altera_s5_ref_mmd.lib alteracl.lib acl_emulator_kern

el_rt.lib pkg_editor.lib libelf.lib acl_hostxml.lib

Thank you.

You should put the output of that command in the linker settings of visual studio. Though, if you don't do this, compilation should fail. Don't you get any warning or errors during compilation of the host code? It seems to me that you are compiling the host code against some other OpenCL SDK (maybe AMD's or Intel's CPU SDK?) or else non-FPGA devices should not at all be detected when you compile using Altera's OpenCL SDK.

Unfortunately I do not have my FPGA environment set up on Windows and hence, I cannot give you exact instructions.

Hi,

Thanks for the hint. I removed the OpenCL.lib which was added by project's default in Visual Studio and kept other libraries I've added before, then it works!

I am facing same issue. If I remove the OpenCL.lib compilation is now failing - as now the cl<Funcs> are not found.

1>ClCompile:

1> options.cpp

1> opencl.cpp

1> main.cpp

1> Generating Code...

1>main.obj : error LNK2019: unresolved external symbol clFinish referenced in function main

1>main.obj : error LNK2019: unresolved external symbol clEnqueueNDRangeKernel referenced in function main

1>main.obj : error LNK2019: unresolved external symbol clSetKernelArg referenced in function main

1>main.obj : error LNK2019: unresolved external symbol clCreateKernel referenced in function "bool __cdecl init(void)" (?init@@YA_NXZ)

1>main.obj : error LNK2019: unresolved external symbol clBuildProgram referenced in function "bool __cdecl init(void)" (?init@@YA_NXZ)

1>main.obj : error LNK2019: unresolved external symbol clCreateCommandQueue referenced in function "bool __cdecl init(void)" (?init@@YA_NXZ)

1>main.obj : error LNK2019: unresolved external symbol clCreateContext referenced in function "bool __cdecl init(void)" (?init@@YA_NXZ)

1>main.obj : error LNK2019: unresolved external symbol clGetPlatformInfo referenced in function "bool __cdecl init(void)" (?init@@YA_NXZ)

1>opencl.obj : error LNK2001: unresolved external symbol clGetPlatformInfo

1>main.obj : error LNK2019: unresolved external symbol clReleaseContext referenced in function "void __cdecl cleanup(void)" (?cleanup@@YAXXZ)

1>main.obj : error LNK2019: unresolved external symbol clReleaseCommandQueue referenced in function "void __cdecl cleanup(void)" (?cleanup@@YAXXZ)

1>main.obj : error LNK2019: unresolved external symbol clReleaseProgram referenced in function "void __cdecl cleanup(void)" (?cleanup@@YAXXZ)

1>main.obj : error LNK2019: unresolved external symbol clReleaseKernel referenced in function "void __cdecl cleanup(void)" (?cleanup@@YAXXZ)

1>main.obj : error LNK2019: unresolved external symbol clGetDeviceInfo referenced in function "void __cdecl display_device_info(struct _cl_device_id *)" (?display_device_info@@YAXPEAU_cl_device_id@@@Z)

1>opencl.obj : error LNK2001: unresolved external symbol clGetDeviceInfo

1>opencl.obj : error LNK2019: unresolved external symbol clGetPlatformIDs referenced in function "struct _cl_platform_id * __cdecl aocl_utils::findPlatform(char const *)" (?findPlatform@aocl_utils@@YAPEAU_cl_platform_id@@PEBD@Z)

1>opencl.obj : error LNK2019: unresolved external symbol clGetDeviceIDs referenced in function "struct _cl_device_id * * __cdecl aocl_utils::getDevices(struct _cl_platform_id *,unsigned __int64,unsigned int *)" (?getDevices@aocl_utils@@YAPEAPEAU_cl_device_id@@PEAU_cl_platform_id@@_KPEAI@Z)

1>opencl.obj : error LNK2019: unresolved external symbol clCreateProgramWithBinary referenced in function "struct _cl_program * __cdecl aocl_utils::createProgramFromBinary(struct _cl_context *,char const *,struct _cl_device_id * const *,unsigned int)" (?createProgramFromBinary@aocl_utils@@YAPEAU_cl_program@@PEAU_cl_context@@PEBDPEBQEAU_cl_device_id@@I@Z)

1>opencl.obj : error LNK2019: unresolved external symbol clGetEventProfilingInfo referenced in function "unsigned __int64 __cdecl aocl_utils::getStartEndTime(struct _cl_event *)" (?getStartEndTime@aocl_utils@@YA_KPEAU_cl_event@@@Z)

1>C:\Users\mmhazra\Desktop\P-CSTN-OPNCL-16-1-v2\eg1\hello_world\bin\host.exe : fatal error LNK1120: 17 unresolved externals

1>

1>Build FAILED.

Hello

You need to add the library name and directory which you run "aocl linkflags" command

You can follow the step to do this

Step1

remove OpenCL.lib from Project->Properites->Linker->Input->Additional Dependencis

add altera_a10_ref_mmd.lib alteracl.lib acl_emulator_kernel_rt.lib pkg_editor.lib libelf.lib acl_hostxml.lib

Step2 add correspond lib's path select Project->Properites->Linker->General->Additional Library Dictories

C:\intelFPGA_pro\17.0\hld\board\a10_ref/windows64/lib;C:/intelFPGA_pro/17.0/hld/host/windows64/lib

Step3 copy the WDAPI1021.dll from your board directory to "C:\Windows\System32"

EX: My reference FPGA board is a10gx so i need to copy wdapi1021.dll from "C:\intelFPGA_pro\17.0\hld\board\a10_ref\windows64\driver" directory to "C:\Windows\System32"

After finishing the steps, you can run the host and get correct result

Querying platform for info:

==========================

CL_PLATFORM_NAME = Intel(R) FPGA SDK for OpenCL(TM)

CL_PLATFORM_VENDOR = Intel(R) Corporation

CL_PLATFORM_VERSION = OpenCL 1.0 Intel(R) FPGA SDK for OpenCL(TM), Version 17.0

Querying device for info:

========================

CL_DEVICE_NAME = EmulatorDevice : Emulated Device

CL_DEVICE_VENDOR = Altera Corporation

CL_DEVICE_VENDOR_ID = 4466

CL_DEVICE_VERSION = OpenCL 1.0 Intel(R) FPGA SDK for OpenCL(TM), Version 17.0

CL_DRIVER_VERSION = 17.0

CL_DEVICE_ADDRESS_BITS = 64

CL_DEVICE_AVAILABLE = true

CL_DEVICE_ENDIAN_LITTLE = true

CL_DEVICE_GLOBAL_MEM_CACHE_SIZE = 32768

CL_DEVICE_GLOBAL_MEM_CACHELINE_SIZE = 0

CL_DEVICE_GLOBAL_MEM_SIZE = 2147483648

............................................................................................................

Command queue out of order? = false

Command queue profiling enabled? = true

Using AOCX: hello_world.aocx

Kernel initialization is complete.

Launching the kernel...

Thread# 2: Hello from Altera's OpenCL Compiler!

Kernel execution is complete.

CL_DEVICE_IMAGE_SUPPORT = true

Good luck