diff --git a/examples/idle.rs b/examples/idle.rs
new file mode 100644
index 0000000000..ddd6326765
--- /dev/null
+++ b/examples/idle.rs
@@ -0,0 +1,31 @@
+//! examples/idle.rs
+
+#![deny(unsafe_code)]
+#![deny(warnings)]
+#![no_main]
+#![no_std]
+
+use panic_semihosting as _;
+
+#[rtic::app(device = lm3s6965)]
+mod app {
+    use cortex_m_semihosting::{debug, hprintln};
+
+    #[init]
+    fn init(_: init::Context) -> (init::LateResources, init::Monotonics) {
+        hprintln!("init").unwrap();
+
+        (init::LateResources {}, init::Monotonics())
+    }
+
+    #[idle]
+    fn idle(_: idle::Context) -> ! {
+        hprintln!("idle").unwrap();
+
+        debug::exit(debug::EXIT_SUCCESS);
+
+        loop {
+            cortex_m::asm::nop();
+        }
+    }
+}
diff --git a/examples/init.rs b/examples/init.rs
new file mode 100644
index 0000000000..9d56d45024
--- /dev/null
+++ b/examples/init.rs
@@ -0,0 +1,32 @@
+//! examples/init.rs
+
+#![deny(unsafe_code)]
+#![deny(warnings)]
+#![no_main]
+#![no_std]
+
+use panic_semihosting as _;
+
+#[rtic::app(device = lm3s6965, peripherals = true)]
+mod app {
+    use cortex_m_semihosting::{debug, hprintln};
+
+    #[init]
+    fn init(cx: init::Context) -> (init::LateResources, init::Monotonics) {
+        // Cortex-M peripherals
+        let _core: cortex_m::Peripherals = cx.core;
+
+        // Device specific peripherals
+        let _device: lm3s6965::Peripherals = cx.device;
+
+        // Access to the critical section token,
+        // to indicate that this is a critical seciton
+        let _cs_token: bare_metal::CriticalSection = cx.cs;
+
+        hprintln!("init").unwrap();
+
+        debug::exit(debug::EXIT_SUCCESS);
+
+        (init::LateResources {}, init::Monotonics())
+    }
+}
diff --git a/examples/late.rs b/examples/late.rs
new file mode 100644
index 0000000000..3f480fb347
--- /dev/null
+++ b/examples/late.rs
@@ -0,0 +1,57 @@
+//! examples/late.rs
+
+#![deny(unsafe_code)]
+#![deny(warnings)]
+#![no_main]
+#![no_std]
+
+use panic_semihosting as _;
+
+#[rtic::app(device = lm3s6965)]
+mod app {
+    use cortex_m_semihosting::{debug, hprintln};
+    use heapless::{
+        consts::*,
+        i,
+        spsc::{Consumer, Producer, Queue},
+    };
+    use lm3s6965::Interrupt;
+
+    // Late resources
+    #[resources]
+    struct Resources {
+        p: Producer<'static, u32, U4>,
+        c: Consumer<'static, u32, U4>,
+        #[task_local]
+        #[init(Queue(i::Queue::new()))]
+        q: Queue<u32, U4>,
+    }
+
+    #[init(resources = [q])]
+    fn init(cx: init::Context) -> (init::LateResources, init::Monotonics) {
+        // static mut Q: Queue<u32, U4> = Queue(i::Queue::new());
+
+        let (p, c) = cx.resources.q.split();
+
+        // Initialization of late resources
+        (init::LateResources { p, c }, init::Monotonics())
+    }
+
+    #[idle(resources = [c])]
+    fn idle(mut c: idle::Context) -> ! {
+        loop {
+            if let Some(byte) = c.resources.c.lock(|c| c.dequeue()) {
+                hprintln!("received message: {}", byte).unwrap();
+
+                debug::exit(debug::EXIT_SUCCESS);
+            } else {
+                rtic::pend(Interrupt::UART0);
+            }
+        }
+    }
+
+    #[task(binds = UART0, resources = [p])]
+    fn uart0(mut c: uart0::Context) {
+        c.resources.p.lock(|p| p.enqueue(42).unwrap());
+    }
+}