interrupt 0.1.4

interrupt
Documentation 
1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36

use crate::{disable_mask, set_mask, MASK_ALL};
use core::ops::Deref;

/// Critical section token.
///
/// The current core is executing code within a critical section.
pub struct CriticalSection<'cs> {
    inner: bare_metal::CriticalSection<'cs>,
    mask: u32,
}
impl<'cs> Default for CriticalSection<'cs> {
    fn default() -> Self {
        Self::new()
    }
}
impl<'cs> CriticalSection<'cs> {
    /// Into a critical section. And exit the critical section, when it drop.
    pub fn new() -> Self {
        let mask = disable_mask(MASK_ALL);
        Self {
            inner: unsafe { bare_metal::CriticalSection::new() },
            mask,
        }
    }
}
impl<'cs> Deref for CriticalSection<'cs> {
    type Target = bare_metal::CriticalSection<'cs>;
    fn deref(&self) -> &Self::Target {
        &self.inner
    }
}
impl<'cs> Drop for CriticalSection<'cs> {
    fn drop(&mut self) {
        unsafe { set_mask(self.mask) };
    }
}