Add kernel launch example

Author: szymon-zadworny

oneapi-rs-sys/build.rs

@@ -53,6 +53,7 @@ fn main() {
         .compile("oneapi-shim");
 
     println!("cargo::rustc-link-lib=sycl");
+    println!("cargo::rustc-link-lib=ze_loader");
     println!("cargo::rustc-link-lib=intlc");
 
     for source in cpp_sources {

oneapi-rs/examples/kernel_launch.rs

@@ -0,0 +1,53 @@
+//
+// Copyright (C) 2026 Intel Corporation
+//
+// Under the MIT License or the Apache License v2.0.
+// See LICENSE-MIT and LICENSE-APACHE for license information.
+// SPDX-License-Identifier: MIT OR Apache-2.0
+//
+
+use oneapi_rs::{buffer::Buffer, kernel_bundle::{KernelArgument, KernelArgumentList}, queue::Queue, usm::{SharedAllocator, UsmAllocator}};
+
+static IOTA_SRC: &str = r#"
+#include <sycl/sycl.hpp>
+namespace syclext = sycl::ext::oneapi;
+namespace syclexp = sycl::ext::oneapi::experimental;
+
+extern "C"
+SYCL_EXT_ONEAPI_FUNCTION_PROPERTY((syclexp::nd_range_kernel<1>))
+void iota(float start, float *ptr) {
+    size_t id = syclext::this_work_item::get_nd_item<1>().get_global_linear_id();
+    ptr[id] = start + static_cast<float>(id);
+}
+"#;
+
+struct IotaArgs<'a> {
+    start: f32,
+    buffer: &'a mut Buffer<f32, UsmAllocator<SharedAllocator>>
+}
+
+unsafe impl<'a> KernelArgumentList<2> for IotaArgs<'a> {
+    unsafe fn as_raw_arg_list(&self) -> [&[u8]; 2] {
+        return [
+            unsafe { self.start.as_raw_arg() },
+            unsafe { self.buffer.as_raw_arg() }
+        ]
+    }
+}
+
+fn main() {
+    let mut queue = Queue::new();
+    let mut buffer = queue.alloc_shared::<f32>(1024).wait();
+
+    let kernel = queue.get_context()
+        .create_kernel_bundle_from_source(IOTA_SRC)
+        .build()
+        .get_kernel("iota");
+
+    unsafe { queue.launch(&kernel, IotaArgs { start: 3.14, buffer: &mut buffer }) }.wait();
+
+    for e in buffer.iter() {
+        print!("{e} ");
+    }
+    println!();
+}