no_std_compat::marker

Trait 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§

1.0.0 · Source§

impl !Sync for Arguments<'_>

Source§

impl !Sync for LocalWaker

Source§

impl Sync for no_std_compat::ffi::c_str::Bytes<'_>

1.0.0 · 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 AtomicI128

1.0.0 · 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 AtomicU128

1.0.0 · Source§

impl Sync for AtomicUsize

1.36.0 · Source§

impl Sync for Waker

Source§

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

1.0.0 · Source§

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

1.0.0 · Source§

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

1.0.0 · Source§

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

1.70.0 · Source§

impl<T> !Sync for OnceCell<T>

1.0.0 · Source§

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

1.0.0 · 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 SyncUnsafeCell<T>
where T: Sync + ?Sized,

1.28.0 · Source§

impl<T> Sync for NonZero<T>

1.31.0 · Source§

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

1.0.0 · Source§

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

1.0.0 · Source§

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

1.0.0 · Source§

impl<T> Sync for no_std_compat::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,

1.0.0 · Source§

impl<T> Sync for AtomicPtr<T>

Source§

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

Auto implementors§

§

impl !Sync for RawWaker

§

impl Sync for AsciiChar

§

impl Sync for no_std_compat::cmp::Ordering

§

impl Sync for Infallible

§

impl Sync for c_void

§

impl Sync for no_std_compat::fmt::Alignment

§

impl Sync for FpCategory

§

impl Sync for IntErrorKind

§

impl Sync for SearchStep

§

impl Sync for no_std_compat::sync::atomic::Ordering

§

impl Sync for AllocError

§

impl Sync for Layout

§

impl Sync for LayoutError

§

impl Sync for TypeId

§

impl Sync for CpuidResult

§

impl Sync for __m128

§

impl Sync for __m128bh

§

impl Sync for __m128d

§

impl Sync for __m128h

§

impl Sync for __m128i

§

impl Sync for __m256

§

impl Sync for __m256bh

§

impl Sync for __m256d

§

impl Sync for __m256h

§

impl Sync for __m256i

§

impl Sync for __m512

§

impl Sync for __m512bh

§

impl Sync for __m512d

§

impl Sync for __m512h

§

impl Sync for __m512i

§

impl Sync for bf16

§

impl Sync for TryFromSliceError

§

impl Sync for no_std_compat::ascii::EscapeDefault

§

impl Sync for BorrowError

§

impl Sync for BorrowMutError

§

impl Sync for CharTryFromError

§

impl Sync for DecodeUtf16Error

§

impl Sync for no_std_compat::char::EscapeDebug

§

impl Sync for no_std_compat::char::EscapeDefault

§

impl Sync for no_std_compat::char::EscapeUnicode

§

impl Sync for ParseCharError

§

impl Sync for ToLowercase

§

impl Sync for ToUppercase

§

impl Sync for TryFromCharError

§

impl Sync for CStr

§

impl Sync for FromBytesUntilNulError

§

impl Sync for FromBytesWithNulError

§

impl Sync for Error

§

impl Sync for SipHasher

§

impl Sync for Assume

§

impl Sync for ParseFloatError

§

impl Sync for ParseIntError

§

impl Sync for TryFromIntError

§

impl Sync for RangeFull

§

impl Sync for no_std_compat::ptr::Alignment

§

impl Sync for ParseBoolError

§

impl Sync for Utf8Error

§

impl Sync for RawWakerVTable

§

impl Sync for Duration

§

impl Sync for TryFromFloatSecsError

§

impl Sync for PhantomPinned

§

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

§

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

§

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

§

impl<'a> Sync for Utf8Pattern<'a>

§

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

§

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

§

impl<'a> Sync for no_std_compat::str::Bytes<'a>

§

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

§

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

§

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

§

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

§

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

§

impl<'a> Sync for no_std_compat::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, 'f> !Sync for VaList<'a, 'f>

§

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

§

impl<'a, A> Sync for no_std_compat::option::IterMut<'a, A>
where A: 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, P> Sync for MatchIndices<'a, P>
where <P as Pattern>::Searcher<'a>: Sync,

§

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

§

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

§

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

§

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

§

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

§

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

§

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

§

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

§

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

§

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

§

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

§

impl<'a, T> Sync for no_std_compat::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, 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 no_std_compat::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 no_std_compat::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 no_std_compat::slice::Split<'a, T, P>
where P: Sync, T: Sync,

§

impl<'a, T, P> Sync for no_std_compat::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 no_std_compat::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 no_std_compat::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<'f> !Sync for VaListImpl<'f>

§

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

§

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

§

impl<A> Sync for no_std_compat::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 C: Sync, B: Sync,

§

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

§

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

§

impl<F> Sync for no_std_compat::iter::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 as Iterator>::Item as IntoIterator>::IntoIter: Sync, I: Sync,

§

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

§

impl<I> Sync for Intersperse<I>
where <I as Iterator>::Item: Sized + Sync, I: 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 I: Sync, F: Sync,

§

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

§

impl<I, F> Sync for Map<I, F>
where I: Sync, F: 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 as Iterator>::Item: Sync, I: 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 I: Sync, F: Sync, St: Sync,

§

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

§

impl<I, const N: usize> Sync for no_std_compat::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 Bound<T>
where T: Sync,

§

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

§

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

§

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

§

impl<T> Sync for AsyncDropInPlace<T>
where <T as AsyncDestruct>::AsyncDestructor: Sync, T: ?Sized,

§

impl<T> Sync for Pending<T>

§

impl<T> Sync for Ready<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 ManuallyDrop<T>
where T: Sync + ?Sized,

§

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

§

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

§

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

§

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

§

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

§

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

§

impl<T, E> Sync for Result<T, E>
where T: Sync, E: 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 no_std_compat::array::IntoIter<T, N>
where T: Sync,

§

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

§

impl<const N: usize> Sync for GetManyMutError<N>