Trait uefi_std::marker::Sync

1.0.0 · source ·
pub unsafe auto trait Sync { }
Expand description

Types for which it is safe to share references between threads.

This trait is automatically implemented when the compiler determines it’s appropriate.

The precise definition is: a type T is Sync if and only if &T is Send. In other words, if there is no possibility of undefined behavior (including data races) when passing &T references between threads.

As one would expect, primitive types like u8 and f64 are all Sync, and so are simple aggregate types containing them, like tuples, structs and enums. More examples of basic Sync types include “immutable” types like &T, and those with simple inherited mutability, such as Box<T>, Vec<T> and most other collection types. (Generic parameters need to be Sync for their container to be Sync.)

A somewhat surprising consequence of the definition is that &mut T is Sync (if T is Sync) even though it seems like that might provide unsynchronized mutation. The trick is that a mutable reference behind a shared reference (that is, & &mut T) becomes read-only, as if it were a & &T. Hence there is no risk of a data race.

A shorter overview of how Sync and Send relate to referencing:

  • &T is Send if and only if T is Sync
  • &mut T is Send if and only if T is Send
  • &T and &mut T are Sync if and only if T is Sync

Types that are not Sync are those that have “interior mutability” in a non-thread-safe form, such as Cell and RefCell. These types allow for mutation of their contents even through an immutable, shared reference. For example the set method on Cell<T> takes &self, so it requires only a shared reference &Cell<T>. The method performs no synchronization, thus Cell cannot be Sync.

Another example of a non-Sync type is the reference-counting pointer Rc. Given any reference &Rc<T>, you can clone a new Rc<T>, modifying the reference counts in a non-atomic way.

For cases when one does need thread-safe interior mutability, Rust provides atomic data types, as well as explicit locking via sync::Mutex and sync::RwLock. These types ensure that any mutation cannot cause data races, hence the types are Sync. Likewise, sync::Arc provides a thread-safe analogue of Rc.

Any types with interior mutability must also use the cell::UnsafeCell wrapper around the value(s) which can be mutated through a shared reference. Failing to doing this is undefined behavior. For example, transmute-ing from &T to &mut T is invalid.

See the Nomicon for more details about Sync.

Implementors§

source§

impl !Sync for LocalWaker

1.6.0 · source§

impl Sync for uefi_std::string::Drain<'_>

source§

impl Sync for AtomicBool

1.34.0 · source§

impl Sync for AtomicI8

1.34.0 · source§

impl Sync for AtomicI16

1.34.0 · source§

impl Sync for AtomicI32

1.34.0 · source§

impl Sync for AtomicI64

source§

impl Sync for AtomicIsize

1.34.0 · source§

impl Sync for AtomicU8

1.34.0 · source§

impl Sync for AtomicU16

1.34.0 · source§

impl Sync for AtomicU32

1.34.0 · source§

impl Sync for AtomicU64

source§

impl Sync for AtomicUsize

1.36.0 · source§

impl Sync for Waker

source§

impl<Dyn> Sync for DynMetadata<Dyn>
where Dyn: ?Sized,

source§

impl<T> !Sync for *const T
where T: ?Sized,

source§

impl<T> !Sync for *mut T
where T: ?Sized,

source§

impl<T> !Sync for Cell<T>
where T: ?Sized,

1.70.0 · source§

impl<T> !Sync for OnceCell<T>

source§

impl<T> !Sync for RefCell<T>
where T: ?Sized,

source§

impl<T> !Sync for UnsafeCell<T>
where T: ?Sized,

1.25.0 · source§

impl<T> !Sync for NonNull<T>
where T: ?Sized,

NonNull pointers are not Sync because the data they reference may be aliased.

source§

impl<T> Sync for ThinBox<T>
where T: Sync + ?Sized,

ThinBox<T> is Sync if T is Sync because the data is owned.

source§

impl<T> Sync for SyncUnsafeCell<T>
where T: Sync + ?Sized,

1.31.0 · source§

impl<T> Sync for ChunksExactMut<'_, T>
where T: Sync,

source§

impl<T> Sync for ChunksMut<'_, T>
where T: Sync,

source§

impl<T> Sync for uefi_std::slice::Iter<'_, T>
where T: Sync,

source§

impl<T> Sync for uefi_std::slice::IterMut<'_, T>
where T: Sync,

1.31.0 · source§

impl<T> Sync for RChunksExactMut<'_, T>
where T: Sync,

1.31.0 · source§

impl<T> Sync for RChunksMut<'_, T>
where T: Sync,

source§

impl<T> Sync for alloc::collections::linked_list::Iter<'_, T>
where T: Sync,

source§

impl<T> Sync for alloc::collections::linked_list::IterMut<'_, T>
where T: Sync,

1.28.0 · source§

impl<T> Sync for NonZero<T>

source§

impl<T> Sync for AtomicPtr<T>

source§

impl<T> Sync for Exclusive<T>
where T: ?Sized,

source§

impl<T, A> !Sync for Rc<T, A>
where A: Allocator, T: ?Sized,

1.4.0 · source§

impl<T, A> !Sync for uefi_std::rc::Weak<T, A>
where A: Allocator, T: ?Sized,

1.6.0 · source§

impl<T, A> Sync for uefi_std::vec::Drain<'_, T, A>
where T: Sync, A: Sync + Allocator,

source§

impl<T, A> Sync for uefi_std::vec::IntoIter<T, A>
where T: Sync, A: Allocator + Sync,

source§

impl<T, A> Sync for Cursor<'_, T, A>
where T: Sync, A: Allocator + Sync,

source§

impl<T, A> Sync for CursorMut<'_, T, A>
where T: Sync, A: Allocator + Sync,

source§

impl<T, A> Sync for LinkedList<T, A>
where T: Sync, A: Allocator + Sync,

1.6.0 · source§

impl<T, A> Sync for alloc::collections::vec_deque::drain::Drain<'_, T, A>
where T: Sync, A: Allocator + Sync,

source§

impl<T, A> Sync for Arc<T, A>
where T: Sync + Send + ?Sized, A: Allocator + Sync,

1.4.0 · source§

impl<T, A> Sync for alloc::sync::Weak<T, A>
where T: Sync + Send + ?Sized, A: Allocator + Sync,

Auto implementors§

§

impl !Sync for LoadedImage

§

impl Sync for Ordering

§

impl Sync for Infallible

§

impl Sync for uefi_std::fmt::Alignment

§

impl Sync for BasicBlock

§

impl Sync for UnwindTerminateReason

§

impl Sync for SearchStep

§

impl Sync for TypeId

§

impl Sync for CpuidResult

§

impl Sync for __m128

§

impl Sync for __m128bh

§

impl Sync for __m128d

§

impl Sync for __m128i

§

impl Sync for __m256

§

impl Sync for __m256bh

§

impl Sync for __m256d

§

impl Sync for __m256i

§

impl Sync for __m512

§

impl Sync for __m512bh

§

impl Sync for __m512d

§

impl Sync for __m512i

§

impl Sync for TryFromSliceError

§

impl Sync for BorrowError

§

impl Sync for BorrowMutError

§

impl Sync for CharTryFromError

§

impl Sync for DecodeUtf16Error

§

impl Sync for uefi_std::char::EscapeDebug

§

impl Sync for uefi_std::char::EscapeDefault

§

impl Sync for uefi_std::char::EscapeUnicode

§

impl Sync for ParseCharError

§

impl Sync for ToLowercase

§

impl Sync for ToUppercase

§

impl Sync for TryFromCharError

§

impl Sync for Error

§

impl Sync for Dir

§

impl Sync for File

§

impl Sync for FileSystem

§

impl Sync for SipHasher

§

impl Sync for ReturnToArg

§

impl Sync for UnwindActionArg

§

impl Sync for Stdout

§

impl Sync for Assume

§

impl Sync for RangeFull

§

impl Sync for Pointer

§

impl Sync for uefi_std::ptr::Alignment

§

impl Sync for Shell

§

impl Sync for ParseBoolError

§

impl Sync for Utf8Error

§

impl Sync for FromUtf8Error

§

impl Sync for FromUtf16Error

§

impl Sync for String

§

impl Sync for PhantomPinned

§

impl<'a> !Sync for Arguments<'a>

§

impl<'a> !Sync for Formatter<'a>

§

impl<'a> Sync for EscapeAscii<'a>

§

impl<'a> Sync for CharSearcher<'a>

§

impl<'a> Sync for Bytes<'a>

§

impl<'a> Sync for CharIndices<'a>

§

impl<'a> Sync for Chars<'a>

§

impl<'a> Sync for EncodeUtf16<'a>

§

impl<'a> Sync for uefi_std::str::EscapeDebug<'a>

§

impl<'a> Sync for uefi_std::str::EscapeDefault<'a>

§

impl<'a> Sync for uefi_std::str::EscapeUnicode<'a>

§

impl<'a> Sync for Lines<'a>

§

impl<'a> Sync for LinesAny<'a>

§

impl<'a> Sync for SplitAsciiWhitespace<'a>

§

impl<'a> Sync for SplitWhitespace<'a>

§

impl<'a> Sync for Utf8Chunk<'a>

§

impl<'a> Sync for Utf8Chunks<'a>

§

impl<'a, 'b> !Sync for DebugList<'a, 'b>

§

impl<'a, 'b> !Sync for DebugMap<'a, 'b>

§

impl<'a, 'b> !Sync for DebugSet<'a, 'b>

§

impl<'a, 'b> !Sync for DebugStruct<'a, 'b>

§

impl<'a, 'b> !Sync for DebugTuple<'a, 'b>

§

impl<'a, 'b> Sync for CharSliceSearcher<'a, 'b>

§

impl<'a, 'b> Sync for StrSearcher<'a, 'b>

§

impl<'a, 'b, const N: usize> Sync for CharArrayRefSearcher<'a, 'b, N>

§

impl<'a, A> Sync for uefi_std::option::Iter<'a, A>
where A: Sync,

§

impl<'a, A> Sync for uefi_std::option::IterMut<'a, A>
where A: Sync,

§

impl<'a, B: ?Sized> Sync for Cow<'a, B>
where B: Sync, <B as ToOwned>::Owned: Sync,

§

impl<'a, F> Sync for CharPredicateSearcher<'a, F>
where F: Sync,

§

impl<'a, I> Sync for ByRefSized<'a, I>
where I: Sync,

§

impl<'a, I, A> Sync for Splice<'a, I, A>
where A: Sync, I: Sync, <I as Iterator>::Item: Sync,

§

impl<'a, P> Sync for MatchIndices<'a, P>
where <P as Pattern<'a>>::Searcher: Sync,

§

impl<'a, P> Sync for Matches<'a, P>
where <P as Pattern<'a>>::Searcher: Sync,

§

impl<'a, P> Sync for RMatchIndices<'a, P>
where <P as Pattern<'a>>::Searcher: Sync,

§

impl<'a, P> Sync for RMatches<'a, P>
where <P as Pattern<'a>>::Searcher: Sync,

§

impl<'a, P> Sync for uefi_std::str::RSplit<'a, P>
where <P as Pattern<'a>>::Searcher: Sync,

§

impl<'a, P> Sync for uefi_std::str::RSplitN<'a, P>
where <P as Pattern<'a>>::Searcher: Sync,

§

impl<'a, P> Sync for RSplitTerminator<'a, P>
where <P as Pattern<'a>>::Searcher: Sync,

§

impl<'a, P> Sync for uefi_std::str::Split<'a, P>
where <P as Pattern<'a>>::Searcher: Sync,

§

impl<'a, P> Sync for uefi_std::str::SplitInclusive<'a, P>
where <P as Pattern<'a>>::Searcher: Sync,

§

impl<'a, P> Sync for uefi_std::str::SplitN<'a, P>
where <P as Pattern<'a>>::Searcher: Sync,

§

impl<'a, P> Sync for SplitTerminator<'a, P>
where <P as Pattern<'a>>::Searcher: Sync,

§

impl<'a, T> Sync for uefi_std::result::Iter<'a, T>
where T: Sync,

§

impl<'a, T> Sync for uefi_std::result::IterMut<'a, T>
where T: Sync,

§

impl<'a, T> Sync for Chunks<'a, T>
where T: Sync,

§

impl<'a, T> Sync for ChunksExact<'a, T>
where T: Sync,

§

impl<'a, T> Sync for RChunks<'a, T>
where T: Sync,

§

impl<'a, T> Sync for RChunksExact<'a, T>
where T: Sync,

§

impl<'a, T> Sync for Windows<'a, T>
where T: Sync,

§

impl<'a, T, F, A> Sync for ExtractIf<'a, T, F, A>
where A: Sync, F: Sync, T: Sync,

§

impl<'a, T, P> Sync for ChunkBy<'a, T, P>
where P: Sync, T: Sync,

§

impl<'a, T, P> Sync for ChunkByMut<'a, T, P>
where P: Sync, T: Sync,

§

impl<'a, T, P> Sync for uefi_std::slice::RSplit<'a, T, P>
where P: Sync, T: Sync,

§

impl<'a, T, P> Sync for RSplitMut<'a, T, P>
where P: Sync, T: Sync,

§

impl<'a, T, P> Sync for uefi_std::slice::RSplitN<'a, T, P>
where P: Sync, T: Sync,

§

impl<'a, T, P> Sync for RSplitNMut<'a, T, P>
where P: Sync, T: Sync,

§

impl<'a, T, P> Sync for uefi_std::slice::Split<'a, T, P>
where P: Sync, T: Sync,

§

impl<'a, T, P> Sync for uefi_std::slice::SplitInclusive<'a, T, P>
where P: Sync, T: Sync,

§

impl<'a, T, P> Sync for SplitInclusiveMut<'a, T, P>
where P: Sync, T: Sync,

§

impl<'a, T, P> Sync for SplitMut<'a, T, P>
where P: Sync, T: Sync,

§

impl<'a, T, P> Sync for uefi_std::slice::SplitN<'a, T, P>
where P: Sync, T: Sync,

§

impl<'a, T, P> Sync for SplitNMut<'a, T, P>
where P: Sync, T: Sync,

§

impl<'a, T, const N: usize> !Sync for ArrayWindows<'a, T, N>

§

impl<'a, T, const N: usize> Sync for uefi_std::slice::ArrayChunks<'a, T, N>
where T: Sync,

§

impl<'a, T, const N: usize> Sync for ArrayChunksMut<'a, T, N>
where T: Sync,

§

impl<'a, const N: usize> Sync for CharArraySearcher<'a, N>

§

impl<'b, T> !Sync for Ref<'b, T>

§

impl<'b, T> !Sync for RefMut<'b, T>

§

impl<A> Sync for Repeat<A>
where A: Sync,

§

impl<A> Sync for RepeatN<A>
where A: Sync,

§

impl<A> Sync for uefi_std::option::IntoIter<A>
where A: Sync,

§

impl<A, B> Sync for Chain<A, B>
where A: Sync, B: Sync,

§

impl<A, B> Sync for Zip<A, B>
where A: Sync, B: Sync,

§

impl<B, C> Sync for ControlFlow<B, C>
where B: Sync, C: Sync,

§

impl<F> Sync for FormatterFn<F>
where F: Sync,

§

impl<F> Sync for FromFn<F>
where F: Sync,

§

impl<F> Sync for OnceWith<F>
where F: Sync,

§

impl<F> Sync for RepeatWith<F>
where F: Sync,

§

impl<H> Sync for BuildHasherDefault<H>

§

impl<I> Sync for DecodeUtf16<I>
where I: Sync,

§

impl<I> Sync for Cloned<I>
where I: Sync,

§

impl<I> Sync for Copied<I>
where I: Sync,

§

impl<I> Sync for Cycle<I>
where I: Sync,

§

impl<I> Sync for Enumerate<I>
where I: Sync,

§

impl<I> Sync for Flatten<I>
where I: Sync, <<I as Iterator>::Item as IntoIterator>::IntoIter: Sync,

§

impl<I> Sync for Fuse<I>
where I: Sync,

§

impl<I> Sync for Intersperse<I>
where I: Sync, <I as Iterator>::Item: Sync,

§

impl<I> Sync for Peekable<I>
where I: Sync, <I as Iterator>::Item: Sync,

§

impl<I> Sync for Skip<I>
where I: Sync,

§

impl<I> Sync for StepBy<I>
where I: Sync,

§

impl<I> Sync for Take<I>
where I: Sync,

§

impl<I, F> Sync for FilterMap<I, F>
where F: Sync, I: Sync,

§

impl<I, F> Sync for Inspect<I, F>
where F: Sync, I: Sync,

§

impl<I, F> Sync for Map<I, F>
where F: Sync, I: Sync,

§

impl<I, F, const N: usize> Sync for MapWindows<I, F, N>
where F: Sync, I: Sync, <I as Iterator>::Item: Sync,

§

impl<I, G> Sync for IntersperseWith<I, G>
where G: Sync, I: Sync, <I as Iterator>::Item: Sync,

§

impl<I, P> Sync for Filter<I, P>
where I: Sync, P: Sync,

§

impl<I, P> Sync for MapWhile<I, P>
where I: Sync, P: Sync,

§

impl<I, P> Sync for SkipWhile<I, P>
where I: Sync, P: Sync,

§

impl<I, P> Sync for TakeWhile<I, P>
where I: Sync, P: Sync,

§

impl<I, St, F> Sync for Scan<I, St, F>
where F: Sync, I: Sync, St: Sync,

§

impl<I, U, F> Sync for FlatMap<I, U, F>
where F: Sync, I: Sync, <U as IntoIterator>::IntoIter: Sync,

§

impl<I, const N: usize> Sync for uefi_std::iter::ArrayChunks<I, N>
where I: Sync, <I as Iterator>::Item: Sync,

§

impl<Idx> Sync for Range<Idx>
where Idx: Sync,

§

impl<Idx> Sync for RangeFrom<Idx>
where Idx: Sync,

§

impl<Idx> Sync for RangeInclusive<Idx>
where Idx: Sync,

§

impl<Idx> Sync for RangeTo<Idx>
where Idx: Sync,

§

impl<Idx> Sync for RangeToInclusive<Idx>
where Idx: Sync,

§

impl<Ptr> Sync for Pin<Ptr>
where Ptr: Sync,

§

impl<T> !Sync for UniqueRc<T>

§

impl<T> Sync for Bound<T>
where T: Sync,

§

impl<T> Sync for Option<T>
where T: Sync,

§

impl<T> Sync for Reverse<T>
where T: Sync,

§

impl<T> Sync for Empty<T>

§

impl<T> Sync for Once<T>
where T: Sync,

§

impl<T> Sync for Rev<T>
where T: Sync,

§

impl<T> Sync for Discriminant<T>

§

impl<T> Sync for Yeet<T>
where T: Sync,

§

impl<T> Sync for uefi_std::result::IntoIter<T>
where T: Sync,

§

impl<T> Sync for MaybeUninit<T>
where T: Sync,

§

impl<T, A> Sync for Vec<T, A>
where A: Sync, T: Sync,

§

impl<T, E> Sync for Result<T, E>
where E: Sync, T: Sync,

§

impl<T, F = fn() -> T> !Sync for LazyCell<T, F>

§

impl<T, F> Sync for Successors<T, F>
where F: Sync, T: Sync,

§

impl<T, const N: usize> Sync for uefi_std::array::IntoIter<T, N>
where T: Sync,

§

impl<T: ?Sized> Sync for ManuallyDrop<T>
where T: Sync,

§

impl<T: ?Sized> Sync for PhantomData<T>
where T: Sync,

§

impl<T: ?Sized, A> Sync for Box<T, A>
where A: Sync, T: Sync,

§

impl<Y, R> Sync for CoroutineState<Y, R>
where R: Sync, Y: Sync,