mbarrier 0.1.3

Cross-platform memory barrier implementations for Rust, inspired by Linux kernel
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

/*!
Generic memory barrier implementations for unsupported architectures.

Provides fallback implementations using Rust's atomic fencing.
*/

use core::sync::atomic::{Ordering, fence};

/// Generic read memory barrier implementation.
///
/// Uses Rust's atomic fence with Acquire ordering.
#[inline(always)]
pub fn rmb_impl() {
    fence(Ordering::Acquire);
}

/// Generic write memory barrier implementation.
///
/// Uses Rust's atomic fence with Release ordering.
#[inline(always)]
pub fn wmb_impl() {
    fence(Ordering::Release);
}

/// Generic memory barrier implementation.
///
/// Uses Rust's atomic fence with SeqCst ordering.
#[inline(always)]
pub fn mb_impl() {
    fence(Ordering::SeqCst);
}