Files

arrayref

lib.rs

arrayvec

array.rsarray_string.rschar.rserrors.rslib.rsmaybe_uninit.rs

bamboo_rs_core

entry

decode

error.rsmod.rs

encode

error.rsmod.rs

publish

error.rsmod.rs

verify

batch.rserror.rsmod.rs

mod.rs

signature

error.rsmod.rs

util

hex_serde.rsmod.rs

lib.rsyamf_hash.rs

blake2b_simd

avx2.rsblake2bp.rsguts.rslib.rsmany.rsportable.rssse41.rs

block_buffer

lib.rs

byteorder

lib.rs

cfg_if

lib.rs

constant_time_eq

lib.rs

cpufeatures

lib.rsx86.rs

crossbeam_channel

flavors

array.rsat.rslist.rsmod.rsnever.rstick.rszero.rs

channel.rscontext.rscounter.rserr.rslib.rsselect.rsselect_macro.rsutils.rswaker.rs

crossbeam_deque

deque.rslib.rs

crossbeam_epoch

sync

list.rsmod.rsqueue.rs

atomic.rscollector.rsdefault.rsdeferred.rsepoch.rsguard.rsinternal.rslib.rs

crossbeam_utils

atomic

atomic_cell.rsconsume.rsmod.rsseq_lock.rs

sync

mod.rsparker.rssharded_lock.rswait_group.rs

backoff.rscache_padded.rslib.rsthread.rs

curve25519_dalek

backend

serial

curve_models

mod.rs

scalar_mul

mod.rspippenger.rsprecomputed_straus.rsstraus.rsvariable_base.rsvartime_double_base.rs

u64

constants.rsfield.rsmod.rsscalar.rs

mod.rs

mod.rs

constants.rsedwards.rsfield.rslib.rsmacros.rsmontgomery.rsprelude.rsristretto.rsscalar.rstraits.rswindow.rs

digest

digest.rsdyn_digest.rserrors.rsfixed.rslib.rsvariable.rsxof.rs

doc_comment

lib.rs

ed25519

lib.rs

ed25519_dalek

batch.rsconstants.rserrors.rskeypair.rslib.rspublic.rssecret.rssignature.rs

either

lib.rs

generic_array

arr.rsfunctional.rshex.rsimpls.rsiter.rslib.rssequence.rs

getrandom

error.rserror_impls.rslib.rslinux_android.rsuse_file.rsutil.rsutil_libc.rs

hex

error.rslib.rs

keccak

lib.rs

lazy_static

inline_lazy.rslib.rs

libc

unix

linux_like

linux

arch

generic

mod.rs

mod.rs

gnu

b64

x86_64

align.rsmod.rsnot_x32.rs

mod.rs

align.rsmod.rs

align.rsmod.rs

mod.rs

align.rsmod.rs

fixed_width_ints.rslib.rsmacros.rs

lipmaa_link

lib.rs

memoffset

lib.rsoffset_of.rsraw_field.rsspan_of.rs

merlin

constants.rslib.rsstrobe.rstranscript.rs

num_cpus

lib.rslinux.rs

opaque_debug

lib.rs

ppv_lite86

x86_64

mod.rssse2.rs

lib.rssoft.rstypes.rs

proc_macro2

detection.rsfallback.rslib.rsmarker.rsparse.rswrapper.rs

quote

ext.rsformat.rsident_fragment.rslib.rsruntime.rsspanned.rsto_tokens.rs

rand

distributions

weighted

alias_method.rsmod.rs

bernoulli.rsbinomial.rscauchy.rsdirichlet.rsexponential.rsfloat.rsgamma.rsinteger.rsmod.rsnormal.rsother.rspareto.rspoisson.rstriangular.rsuniform.rsunit_circle.rsunit_sphere.rsutils.rsweibull.rsziggurat_tables.rs

rngs

adapter

mod.rsread.rsreseeding.rs

entropy.rsmock.rsmod.rsstd.rsthread.rs

seq

index.rsmod.rs

lib.rsprelude.rs

rand_chacha

chacha.rsguts.rslib.rs

rand_core

block.rserror.rsimpls.rsle.rslib.rsos.rs

rayon

collections

binary_heap.rsbtree_map.rsbtree_set.rshash_map.rshash_set.rslinked_list.rsmod.rsvec_deque.rs

compile_fail

cannot_collect_filtermap_data.rscannot_zip_filtered_data.rscell_par_iter.rsmod.rsmust_use.rsno_send_par_iter.rsrc_par_iter.rs

iter

collect

consumer.rsmod.rs

find_first_last

mod.rs

plumbing

mod.rs

chain.rschunks.rscloned.rscopied.rsempty.rsenumerate.rsextend.rsfilter.rsfilter_map.rsfind.rsflat_map.rsflat_map_iter.rsflatten.rsflatten_iter.rsfold.rsfor_each.rsfrom_par_iter.rsinspect.rsinterleave.rsinterleave_shortest.rsintersperse.rslen.rsmap.rsmap_with.rsmod.rsmultizip.rsnoop.rsonce.rspanic_fuse.rspar_bridge.rspositions.rsproduct.rsreduce.rsrepeat.rsrev.rsskip.rssplitter.rsstep_by.rssum.rstake.rstry_fold.rstry_reduce.rstry_reduce_with.rsunzip.rsupdate.rswhile_some.rszip.rszip_eq.rs

slice

mergesort.rsmod.rsquicksort.rs

array.rsdelegate.rslib.rsmath.rsoption.rspar_either.rsprelude.rsprivate.rsrange.rsrange_inclusive.rsresult.rssplit_producer.rsstr.rsstring.rsvec.rs

rayon_core

compile_fail

mod.rsquicksort_race1.rsquicksort_race2.rsquicksort_race3.rsrc_return.rsrc_upvar.rsscope_join_bad.rs

join

mod.rs

scope

mod.rs

sleep

counters.rsmod.rs

spawn

mod.rs

thread_pool

mod.rs

job.rslatch.rslib.rslog.rsprivate.rsregistry.rsunwind.rs

scopeguard

lib.rs

serde

de

ignored_any.rsimpls.rsmod.rsseed.rsutf8.rsvalue.rs

private

de.rsdoc.rsmod.rsser.rssize_hint.rs

ser

fmt.rsimpls.rsimpossible.rsmod.rs

integer128.rslib.rsmacros.rs

serde_bytes

bytebuf.rsbytes.rsde.rslib.rsser.rs

serde_derive

internals

ast.rsattr.rscase.rscheck.rsctxt.rsmod.rsreceiver.rsrespan.rssymbol.rs

bound.rsde.rsdummy.rsfragment.rslib.rspretend.rsser.rstry.rs

sha2

sha256

soft.rsx86.rs

sha512

soft.rs

consts.rslib.rssha256.rssha512.rs

signature

error.rslib.rssignature.rssigner.rsverifier.rs

snafu

backtrace_inert.rslib.rs

snafu_derive

lib.rsshared.rs

static_assertions

assert_cfg.rsassert_eq_size.rsassert_eq_type.rsassert_fields.rsassert_impl.rsassert_ne_type.rsassert_not_impl.rsassert_obj_safe.rsconst_assert.rslib.rs

subtle

lib.rs

syn

gen

clone.rsdebug.rseq.rsgen_helper.rshash.rsvisit.rs

attr.rsawait.rsbigint.rsbuffer.rscustom_keyword.rscustom_punctuation.rsdata.rsderive.rsdiscouraged.rserror.rsexport.rsexpr.rsext.rsfile.rsgenerics.rsgroup.rsident.rsitem.rslib.rslifetime.rslit.rslookahead.rsmac.rsmacros.rsop.rsparse.rsparse_macro_input.rsparse_quote.rspat.rspath.rsprint.rspunctuated.rsreserved.rssealed.rsspan.rsspanned.rsstmt.rsthread.rstoken.rstt.rsty.rsverbatim.rswhitespace.rs

synstructure

lib.rsmacros.rs

typenum

array.rsbit.rsint.rslib.rsmarker_traits.rsoperator_aliases.rsprivate.rstype_operators.rsuint.rs

unicode_xid

lib.rstables.rs

varu64

lib.rsnb.rs

yamf_hash

util

hex_serde.rsmod.rs

error.rslib.rs

zeroize

lib.rsx86.rs

zeroize_derive

lib.rs

>

//! [`Zeroize`] impls for x86 SIMD registers

use crate::{atomic_fence, volatile_write, Zeroize};

#[cfg(target_arch = "x86")]
use core::arch::x86::*;

#[cfg(target_arch = "x86_64")]
use core::arch::x86_64::*;

macro_rules! impl_zeroize_for_simd_register {
    ($type:ty, $feature:expr, $zero_value:ident) => {
        #[cfg_attr(docsrs, doc(cfg(target_arch = "x86")))] // also `x86_64`
        #[cfg_attr(docsrs, doc(cfg(target_feature = $feature)))]
        impl Zeroize for $type {
            fn zeroize(&mut self) {
                volatile_write(self, unsafe { $zero_value() });
                atomic_fence();
            }
        }
    };
}

#[cfg(target_feature = "sse")]
impl_zeroize_for_simd_register!(__m128, "sse", _mm_setzero_ps);

#[cfg(target_feature = "sse2")]
impl_zeroize_for_simd_register!(__m128d, "sse2", _mm_setzero_pd);

#[cfg(target_feature = "sse2")]
impl_zeroize_for_simd_register!(__m128i, "sse2", _mm_setzero_si128);

#[cfg(target_feature = "avx")]
impl_zeroize_for_simd_register!(__m256, "avx", _mm256_setzero_ps);

#[cfg(target_feature = "avx")]
impl_zeroize_for_simd_register!(__m256d, "avx", _mm256_setzero_pd);

#[cfg(target_feature = "avx")]
impl_zeroize_for_simd_register!(__m256i, "avx", _mm256_setzero_si256);