DPC的怪异行为在FPGA设备上运行它后代码

Question

我正在使用DPC ++在FPGA设备上加速KNN算法。以下代码是我为欧几里得距离编写的代码。问题在于，在FPGA硬件（Intel Arria 10 Oneapi）上运行时，FPGA_EMULATION效果很好，没有问题给出了结果缓冲区中的所有值，这意味着在Parallel_for lioop中出现了错误。但是我找不到任何错误，仿真奏效了。

我正在使用Intel DevCloud平台。

std::vector<double> distance_calculation_FPGA(queue& q, const std::vector<std::vector<double>>& dataset, const std::vector<double>& curr_test) {
    std::cout<<"convert 2D to 1D"<<std::endl;
    std::vector<double>linear_dataset;
    for (int i = 0; i < dataset.size(); ++i) {
        for (int j = 0; j < dataset[i].size(); ++j) {
            linear_dataset.push_back(dataset[i][j]);
        }
    }
    std::cout<<"buffering"<<std::endl;
      range<1> num_items{dataset.size()};
    std::vector<double>res;
    //std::cout << "im in" << std::endl;

    res.resize(dataset.size());
    buffer dataset_buf(linear_dataset);
    buffer curr_test_buf(curr_test);
    buffer res_buf(res.data(), num_items);
    
    std::cout<<"submit a job"<<std::endl;
    auto start = std::chrono::high_resolution_clock::now();
    {
    q.submit([&](handler& h) {
        accessor a(dataset_buf, h, read_only);
        accessor b(curr_test_buf, h, read_only);

        accessor dif(res_buf, h, write_only, no_init);
        h.parallel_for(num_items, [=](auto i) {
                for (int j = 0; j < 5; ++j) {
                    dif[i] += (b[j] - a[i * 5 + j]) * (b[j] - a[i * 5 + j]);  
                }
           // out << "i : " << i << " i[0]: " << i[0] << " b: " << b[0] << cl::sycl::endl;
            });
        }).wait();
    }
    auto finish = std::chrono::high_resolution_clock::now();
    std::chrono::duration<double> elapsed = finish - start;
    std::cout << "Elapsed time: " << elapsed.count() << " s\n";
    /* Iterative distance calculation
        for (int i = 0; i < dataset.size(); ++i) {
            double dis = 0;
            for (int j = 0; j < dataset[i].size(); ++j) {
                dis += (curr_test[j] - dataset[i][j]) * (curr_test[j] - dataset[i][j]);
            }
            res.push_back(dis);
        }
        */
    return res;
}

带有fpga_emulation的结果：./knn.fpga_emu

fpga硬件的结果：./knn.fpga

Answer 1

关于您的使用情况的问题，通常与NAN之类的东西，显然我们正在研究非初始化的内存（或除以0，而您没有）。范围是否有可能在FGPA和/或值不正确初始化数组发病的值？

抱歉，我知道这很基本，但是没有您的数据集，我不能100％确定我可以复制它。