From 596cf585ea8dc278d88e0652dffbacbc75de04c6 Mon Sep 17 00:00:00 2001
From: Jorge Aparicio <jorge@japaric.io>
Date: Mon, 24 Jun 2019 14:09:12 +0200
Subject: Monotonic trait is safe; add MultiCore trait

---
 heterogeneous/src/lib.rs | 6 ++++--
 1 file changed, 4 insertions(+), 2 deletions(-)

(limited to 'heterogeneous/src')

diff --git a/heterogeneous/src/lib.rs b/heterogeneous/src/lib.rs
index a4f0ec5..3288bfe 100644
--- a/heterogeneous/src/lib.rs
+++ b/heterogeneous/src/lib.rs
@@ -8,7 +8,7 @@ use core::{
 };
 
 use bare_metal::Nr;
-use rtfm::Monotonic;
+use rtfm::{Monotonic, MultiCore};
 
 // both cores have the exact same interrupts
 pub use Interrupt_0 as Interrupt_1;
@@ -21,7 +21,7 @@ pub fn xpend(_core: u8, _interrupt: impl Nr) {}
 /// Fake monotonic timer
 pub struct MT;
 
-unsafe impl Monotonic for MT {
+impl Monotonic for MT {
     type Instant = Instant;
 
     fn ratio() -> u32 {
@@ -41,6 +41,8 @@ unsafe impl Monotonic for MT {
     }
 }
 
+impl MultiCore for MT {}
+
 #[derive(Clone, Copy, Eq, PartialEq)]
 pub struct Instant(i32);
 
-- 
cgit v1.2.3