sycl代码需显式指定设备类型、内存访问模式与同步机制，非自动适配；kernel须用accessor访问内存，fpga支持依赖后端，异构同步需显式barrier。
SYCL代码必须显式声明设备类型，不能靠运行时自动选择
SYCL不是“写一次、到处运行”的魔法。queue 构造时必须明确指定目标设备，否则默认回退到主机 CPU（host_selector），哪怕你机器装着 NVIDIA GPU 也不会自动用上。常见错误是只写 queue q;，结果全程在 CPU 上跑，还纳闷为什么没加速。
实操建议：
立即学习“C++免费学习笔记（深入）”；
- 用
gpu_selector前先确认驱动和运行时支持：Intel GPU 用intel_gpu_selector，AMD GPU 需 ROCm +amd_gpu_selector（非标准，依赖实现），NVIDIA GPU 目前仅通过 CUDA Backend（如 AdaptiveCpp 或 DPC++ 的实验性支持）； - FPGA 需要厂商特定后端（如 Intel FPGA Offline Compiler）+ 显式指定
heterogeneous_selector或自定义 selector； - 安全兜底写法：
queue q{gpu_selector{}, [](exception_list l) { for (auto &e : l) std::rethrow_exception(e); }};避免异常被静默吞掉。
kernel 必须定义在 host 代码可见作用域，且不能捕获局部栈变量
SYCL kernel（无论是 parallel_for 还是 single_task）本质是被编译器提取并发送到设备执行的独立单元。它看不到 host 函数的栈帧，所以 [&] 捕获或直接使用未声明为 cl::sycl::accessor 的局部变量会编译失败或运行时崩溃。
实操建议：
立即学习“C++免费学习笔记（深入）”；
- 所有需要在 device 上读写的内存，必须通过
buffer+accessor显式声明生命周期和访问模式； - 小常量（如数组长度、缩放系数）可按值传递进 lambda，但注意大小：超过几个 int 的结构体建议改用
buffer<t></t>创建零维 buffer； - 避免在 kernel lambda 内调用非 SYCL 标准函数（如
std::cout、malloc），设备端不支持； - 示例正确写法：
buffer<int> buf(data, range<1>(N)); q.submit([&](handler& h) { auto acc = buf.get_access<access::mode::read_write>(h); h.parallel_for(range<1>(N), [=](id<1> i) { acc[i] = acc[i] * 2; // OK: 通过 accessor 访问 }); });
DPC++ 和 AdaptiveCpp 对 FPGA 支持路径完全不同
Khronos SYCL 标准本身不规定 FPGA 编译流程，实际支持高度依赖实现。DPC++（Intel）和 AdaptiveCpp（formerly hipSYCL）走的是两条技术路线，不能混用。
实操建议：
立即学习“C++免费学习笔记（深入）”；
- Intel FPGA：必须用 DPC++ +
-fintelfpga，源码需加[[intel::fpga_memory("mlab")]]等属性，且最终生成的是 AOCX 文件，不是可执行 ELF； - AdaptiveCpp 支持 Xilinx FPGA（Vitis Flow），但需手动导出为 XO，再由 Vitis 链接；它不识别 DPC++ 的 FPGA 属性语法；
- 没有通用的
#ifdef __FPGA__宏——不同后端定义的宏不同（DPC++ 用__SYCL_DEVICE_ONLY__，AdaptiveCpp 可能用__HIPSYCL__），跨后端条件编译务必查文档； - FPGA kernel 无法动态调度，所有并行度、流水线深度必须在编译期确定，
range(N)中的N最好是编译期常量。
异构同步靠 explicit barrier，不能依赖语句顺序
CPU 和设备内存空间分离，queue::submit() 是异步发起，不阻塞 host 线程。你以为 submit 后变量就更新了？其实只是把任务扔进命令队列，真正执行可能延后几毫秒。常见 bug 是 submit 后立刻读 buffer 数据，得到未初始化值。
实操建议：
立即学习“C++免费学习笔记（深入）”；
- 强制同步用
q.wait()，但会阻塞 host；更高效的是用event链式等待：auto e = q.submit(...); e.wait();； - 多个 kernel 间有数据依赖？别靠 submit 顺序，用
depends_on(e)显式声明依赖链； - 从 device 拷回数据，最简方式是
host_accessor构造时传read_only_host_task模式，它会自动隐式同步； - 注意：SYCL 2020 引入
wait_and_throw()，比wait()更早暴露 device 端异常，推荐替代。
SYCL 单源的关键不在“写一遍”，而在“每处设备决策都显式可控”。最容易被忽略的是 accessor 的 access mode 和 buffer 生命周期管理——写错一个 access::mode::read 当成 write，轻则结果错，重则触发 OpenCL 驱动 assertion crash。
