oneAPI on Cyclone10gx

I was following this:

https://www.intel.com/content/www/us/en/docs/oneapi-base-toolkit/get-started-guide-linux/2024-0/run-a-sample-project-using-the-command-line.html

and indeed I can compile with make (both emulation and fpga), the issue I experience is at runtime, when I try to execute the ./simple-add-buffers.fpga (previously I had issued cmake .. -DFPGA_DEVICE=cyclone10gx to really target my device).

Overall, I have a dual boot computer with windows10/ubuntu, on windows10 I was able to compile and download a sample vhdl to the fpga, so I am sure the board is powered ok/jtag cable is ok too, I am wondering if on ubuntu any additional driver/os related has to be installed. At the moment I have quartus prime (licence is ok) and oneAPI (on both windows10 and ubuntu). I would prefer Linux as I am more comfortable with command line, but I think I am missing something how to get the Cyclone 10gx board properly installed (my understanding was Quartus prime pro contains the cyclone10 driver..), what should I check to make sure my fpga is configured properly on my linux system?

thanks!

I am trying to compile and run this sample code:

#include <CL/sycl.hpp>
#include <iostream>
#include <sycl/ext/intel/fpga_extensions.hpp>

using namespace cl::sycl;

int main() {
    auto selector = sycl::ext::intel::fpga_selector_v;
    queue q(selector);

    const int N = 100;
    int a[N], b[N], c[N];

    // Initialize arrays on the host
    for (int i = 0; i < N; i++) {
        a[i] = i;
        b[i] = i * 2;
    }

    buffer<int, 1> buf_a(a, range<1>(N));  // Create buffers for arrays
    buffer<int, 1> buf_b(b, range<1>(N));
    buffer<int, 1> buf_c(c, range<1>(N));

    q.submit([&](handler& h) {
        auto a_acc = buf_a.get_access<access::mode::read>(h);
        auto b_acc = buf_b.get_access<access::mode::read>(h);
        auto c_acc = buf_c.get_access<access::mode::write>(h);

        h.parallel_for(range<1>(N), [=](id<1> i) {
            c_acc[i] = a_acc[i] + b_acc[i];  // Perform element-wise addition
        });
    });

    q.wait();  // Wait for completion

    // Print results on the host
    for (int i = 0; i < N; i++) {
        std::cout << c[i] << " ";
    }
    std::cout << std::endl;

    return 0;
}

following your link/suggestion I did add the proper flags (see below), I also made sure the board is seen by the OS but I still get the following runtime error:

tetto@ubuntuoffice:~/mytrial1$ jtagconfig
1) USB-BlasterII [1-1]
  031820DD   10M08SA(.|ES)/10M08S(C|L)
  02E120DD   10CX220Y

tetto@ubuntuoffice:~/mytrial1$ icpx -fsycl -fintelfpga fpga_add2.cpp -Xshardware -Xstarget=Cyclone10GX -o fpga_compile.>aoc: Compiling for FPGA. This process may take several hours to complete.  Prior to performing this compile, be sure to>

tetto@ubuntuoffice:~/mytrial1$ ./fpga_compile.fpga
terminate called after throwing an instance of 'sycl::_V1::runtime_error'
  what():  Invalid device program image: size is zero -30 (PI_ERROR_INVALID_VALUE)
Aborted (core dumped)

latest version of oneAPI:

tetto@ubuntuoffice:~/mytrial1$ icpx --version
Intel(R) oneAPI DPC++/C++ Compiler 2024.0.2 (2024.0.2.20231213)
Target: x86_64-unknown-linux-gnu
Thread model: posix
InstalledDir: /opt/intel/oneapi/compiler/2024.0/bin/compiler
Configuration file: /opt/intel/oneapi/compiler/2024.0/bin/compiler/../icpx.cfg

I have both artus 23.4 (I know not compatible/supported by oneAPI latest yet) and Quartus 23.1 (this should be compatible). My licence is Pro, here is my .bashrc file (do I miss anything there?)

export QSYS_ROOTDIR="/home/tetto/intelFPGA_pro/23.1/qsys/bin"
export QUARTUS_ROOTDIR_OVERRIDE=/home/tetto/intelFPGA_pro/23.1/quartus
export LD_LIBRARY_PATH=~/intelFPGA_pro/23.1/quartus/linux64:$LD_LIBRARY_PATH
export CL_CONTEXT_MPSIM_DEVICE_INTELFPGA=1
export PATH=$PATH:/home/tetto/intelFPGA_pro/23.1/quartus/bin/
export INTELFPGAOCLSDKROOT="/home/tetto/intelFPGA_pro/23.1/hld"

p.s. It just occurred to me, that my machine CPU is non Intel (AMD Ryzen Threadripper 3960X 24-Core Processor), I would think that not an issue, isn't it?

not sure I understand what you wrote, did you try to compile using the same compilation flags I used? If you are successful then the issue is not the compilation flag but some libraries or environment variable? You mention xstarget, is there any documentation?

If you review my post on ‎12-31-2023 10:18 PM I had used that very same compilation flag with the very same syntax as in the online document you posted, I add here below the line I had used on ‎12-31-2023 10:18 PM (that fails at runtime):

tetto@ubuntuoffice:~/mytrial1$ icpx -fsycl -fintelfpga fpga_add2.cpp -Xshardware -Xstarget=Cyclone10GX -o fpga_compile.>aoc: Compiling for FPGA. This process may take several hours to complete.  Prior to performing this compile, be sure to>

tetto@ubuntuoffice:~/mytrial1$ ./fpga_compile.fpga
terminate called after throwing an instance of 'sycl::_V1::runtime_error'
  what():  Invalid device program image: size is zero -30 (PI_ERROR_INVALID_VALUE)
Aborted (core dumped)

---

@BoonBengT_Altera wrote:

Hi @StefanoC,

Recall that previously there was a mention the use of -DFPGA_DEVICE for the compilation command.

However that flag might be obsolete and suspect it might cause some problem.

Hence would suggest to use the -Xstarget instead, more details can be found in the link below:

- https://www.intel.com/content/www/us/en/docs/oneapi/programming-guide/2023-0/fpga-compilation-flags.html

Best Wishes

BB

---

@BoonBengT_Altera on my end still same error:

tetto@ubuntuoffice:~/mytrial1$ ./code.fpga
terminate called after throwing an instance of 'sycl::_V1::runtime_error'
  what():  Invalid device program image: size is zero -30 (PI_ERROR_INVALID_VALUE)
Aborted (core dumped)

what did you modify on line8? can you share your code that you got it to run?

changing that line8 into emulation results in this runtime error:

tetto@ubuntuoffice:~/mytrial1$ ./code-compile.fpga_emu
terminate called after throwing an instance of 'sycl::_V1::runtime_error'
  what():  Native API failed. Native API returns: -2 (PI_ERROR_DEVICE_NOT_AVAILABLE) -2 (PI_ERROR_DEVICE_NOT_AVAILABLE)
Aborted (core dumped)
tetto@ubuntuoffice:~/mytrial1$

however, on your end why did you switch to emulation? Does it work on the real fpga hardware without emulation?

the github repository you pointed is full of codes, but in all the README files I can read I never see Cyclone 10GX as supported, so now I am puzzled. Can you point a simple example that is tested on the Cyclone10 GX (hardware compilation)?

Since you can run (at least the emulation) my sample code while I get an error even with simulation I would think my setup has an issue, is there any library/settings to be checked? Ultimately, on your end, if you turn line8 the way it was, does it work at runtime?

Ok, I gave it a try to the part1. I was able to compile and run it via emulation, but when I tried the cmake with -DFPGA_DEVICE setting to "Cylone10gx" it said "Ignoring as not applicable" (I also tried Cyclone, CycloneGX), how to target my hardware and run it hardware rather than emulated?

tetto@ubuntuoffice:~/oneAPI-samples/DirectProgramming/C++SYCL_FPGA/Tutorials/GettingStarted/fpga_compile/part1_cpp/build$ cmake .. -DFPGA_DEVICE=Cyclone10gx
cmake: /home/tetto/intelFPGA_pro/23.1/quartus/linux64/libcurl.so.4: no version information available (required by cmake)
-- Ignoring FPGA_DEVICE: Cyclone10gx, not applicable
-- Configuring done
-- Generating done
-- Build files have been written to: /home/tetto/oneAPI-samples/DirectProgramming/C++SYCL_FPGA/Tutorials/GettingStarted/fpga_compile/part1_cpp/build