Only emit inline-assembly when building for AVR

Cargo.toml

@@ -17,6 +17,9 @@ include = [
     "/README.md",
 ]
 
+[package.metadata.docs.rs]
+all-features = true
+
 [features]
 atmega1280 = []
 atmega168 = []
@@ -32,11 +35,9 @@ rt = ["avr-device-macros"]
 [dependencies]
 bare-metal = "0.2.5"
 vcell = "0.1.2"
+cfg-if = "0.1.10"
 
 [dependencies.avr-device-macros]
 path = "macros/"
 version = "=0.2.0"
 optional = true
-
-[package.metadata.docs.rs]
-all-features = true

src/asm.rs

@@ -3,17 +3,35 @@
 /// No Operation
 #[inline(always)]
 pub fn nop() {
-    unsafe { llvm_asm!("nop") }
+    cfg_if::cfg_if! {
+        if #[cfg(target_arch = "avr")] {
+            unsafe { llvm_asm!("nop") }
+        } else {
+            unimplemented!()
+        }
+    }
 }
 
 /// Sleep / Wait For Interrupt
 #[inline(always)]
 pub fn sleep() {
-    unsafe { llvm_asm!("sleep") }
+    cfg_if::cfg_if! {
+        if #[cfg(target_arch = "avr")] {
+            unsafe { llvm_asm!("sleep") }
+        } else {
+            unimplemented!()
+        }
+    }
 }
 
 /// Watchdog Reset
 #[inline(always)]
 pub fn wdr() {
-    unsafe { llvm_asm!("wdr") }
+    cfg_if::cfg_if! {
+        if #[cfg(target_arch = "avr")] {
+            unsafe { llvm_asm!("wdr") }
+        } else {
+            unimplemented!()
+        }
+    }
 }

src/interrupt.rs

@@ -13,10 +13,12 @@ pub use bare_metal::{CriticalSection, Mutex, Nr};
 #[inline]
 /// Disables all interrupts
 pub fn disable() {
-    unsafe {
-        llvm_asm!(
-            "cli" :::: "volatile"
-        );
+    cfg_if::cfg_if! {
+        if #[cfg(target_arch = "avr")] {
+            unsafe { llvm_asm!("cli" :::: "volatile") };
+        } else {
+            unimplemented!()
+        }
     }
 }
 
@@ -27,9 +29,13 @@ pub fn disable() {
 ///
 /// - Do not call this function inside an [crate::interrupt::free] critical section
 pub unsafe fn enable() {
-    llvm_asm!(
-        "sei" :::: "volatile"
-    );
+    cfg_if::cfg_if! {
+        if #[cfg(target_arch = "avr")] {
+            llvm_asm!("sei" :::: "volatile");
+        } else {
+            unimplemented!()
+        }
+    }
 }
 
 /// Execute closure `f` in an interrupt-free context.
@@ -39,28 +45,29 @@ pub fn free<F, R>(f: F) -> R
 where
     F: FnOnce(&CriticalSection) -> R,
 {
-    let sreg: u8;
+    cfg_if::cfg_if! {
+        if #[cfg(target_arch = "avr")] {
+            let sreg: u8;
 
-    // Store current state
-    unsafe {
-        llvm_asm!(
-            "in $0,0x3F"
-            : "=r"(sreg)
-            :
-            :
-            : "volatile"
-        );
-    }
+            // Store current state
+            unsafe {
+                llvm_asm!("in $0,0x3F" :"=r"(sreg) ::: "volatile");
+            }
 
-    // Disable interrupts
-    disable();
+            // Disable interrupts
+            disable();
 
-    let r = f(unsafe { &CriticalSection::new() });
+            let r = f(unsafe { &CriticalSection::new() });
 
-    // Restore interrupt state
-    if sreg & 0x80 != 0x00 {
-        unsafe { enable(); }
-    }
+            // Restore interrupt state
+            if sreg & 0x80 != 0x00 {
+                unsafe { enable(); }
+            }
 
-    r
+            r
+        } else {
+            let _ = f;
+            unimplemented!()
+        }
+    }
 }