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
32
33
34
35
36
37
38
39
40
41
42

/*!
Performance comparison example.

This example compares the performance of different barrier types
and demonstrates the overhead they introduce.
*/

use std::time::Instant;

use mbarrier::*;

const ITERATIONS: usize = 1_000_000;

fn benchmark_barrier<F: Fn()>(name: &str, barrier_fn: F) {
    let start = Instant::now();
    // Simple benchmark that just runs the barriers
    // In a no_std environment, we can't measure time precisely
    for _ in 0..ITERATIONS {
        barrier_fn();
    }
    let duration = start.elapsed();
    println!("{}: {} ms", name, duration.as_millis());
}

fn main() {
    // Benchmark no-op (baseline)
    benchmark_barrier("No-op baseline", || {});

    // Benchmark read barriers
    benchmark_barrier("rmb()", rmb);
    benchmark_barrier("smp_rmb()", smp_rmb);

    // Benchmark write barriers
    benchmark_barrier("wmb()", wmb);
    benchmark_barrier("smp_wmb()", smp_wmb);

    // Benchmark general barriers
    benchmark_barrier("mb()", mb);
    benchmark_barrier("smp_mb()", smp_mb);

    // Benchmark completed successfully if we reach here
}