/openbsd/gnu/llvm/llvm/lib/Support/BLAKE3/ |
H A D | blake3_avx2.c | 194 out[0] = loadu(&inputs[0][block_offset + 0 * sizeof(__m256i)]); in transpose_msg_vecs() 195 out[1] = loadu(&inputs[1][block_offset + 0 * sizeof(__m256i)]); in transpose_msg_vecs() 196 out[2] = loadu(&inputs[2][block_offset + 0 * sizeof(__m256i)]); in transpose_msg_vecs() 197 out[3] = loadu(&inputs[3][block_offset + 0 * sizeof(__m256i)]); in transpose_msg_vecs() 198 out[4] = loadu(&inputs[4][block_offset + 0 * sizeof(__m256i)]); in transpose_msg_vecs() 199 out[5] = loadu(&inputs[5][block_offset + 0 * sizeof(__m256i)]); in transpose_msg_vecs() 200 out[6] = loadu(&inputs[6][block_offset + 0 * sizeof(__m256i)]); in transpose_msg_vecs() 201 out[7] = loadu(&inputs[7][block_offset + 0 * sizeof(__m256i)]); in transpose_msg_vecs() 202 out[8] = loadu(&inputs[0][block_offset + 1 * sizeof(__m256i)]); in transpose_msg_vecs() 203 out[9] = loadu(&inputs[1][block_offset + 1 * sizeof(__m256i)]); in transpose_msg_vecs() [all …]
|
H A D | blake3_neon.c | 200 out[0] = loadu_128(&inputs[0][block_offset + 0 * sizeof(uint32x4_t)]); in transpose_msg_vecs4() 201 out[1] = loadu_128(&inputs[1][block_offset + 0 * sizeof(uint32x4_t)]); in transpose_msg_vecs4() 202 out[2] = loadu_128(&inputs[2][block_offset + 0 * sizeof(uint32x4_t)]); in transpose_msg_vecs4() 203 out[3] = loadu_128(&inputs[3][block_offset + 0 * sizeof(uint32x4_t)]); in transpose_msg_vecs4() 204 out[4] = loadu_128(&inputs[0][block_offset + 1 * sizeof(uint32x4_t)]); in transpose_msg_vecs4() 205 out[5] = loadu_128(&inputs[1][block_offset + 1 * sizeof(uint32x4_t)]); in transpose_msg_vecs4() 206 out[6] = loadu_128(&inputs[2][block_offset + 1 * sizeof(uint32x4_t)]); in transpose_msg_vecs4() 207 out[7] = loadu_128(&inputs[3][block_offset + 1 * sizeof(uint32x4_t)]); in transpose_msg_vecs4() 208 out[8] = loadu_128(&inputs[0][block_offset + 2 * sizeof(uint32x4_t)]); in transpose_msg_vecs4() 209 out[9] = loadu_128(&inputs[1][block_offset + 2 * sizeof(uint32x4_t)]); in transpose_msg_vecs4() [all …]
|
H A D | blake3_avx512.c | 1025 out[0] = loadu_512(&inputs[0][block_offset]); in transpose_msg_vecs16() 1026 out[1] = loadu_512(&inputs[1][block_offset]); in transpose_msg_vecs16() 1027 out[2] = loadu_512(&inputs[2][block_offset]); in transpose_msg_vecs16() 1028 out[3] = loadu_512(&inputs[3][block_offset]); in transpose_msg_vecs16() 1029 out[4] = loadu_512(&inputs[4][block_offset]); in transpose_msg_vecs16() 1030 out[5] = loadu_512(&inputs[5][block_offset]); in transpose_msg_vecs16() 1031 out[6] = loadu_512(&inputs[6][block_offset]); in transpose_msg_vecs16() 1032 out[7] = loadu_512(&inputs[7][block_offset]); in transpose_msg_vecs16() 1033 out[8] = loadu_512(&inputs[8][block_offset]); in transpose_msg_vecs16() 1034 out[9] = loadu_512(&inputs[9][block_offset]); in transpose_msg_vecs16() [all …]
|
H A D | blake3_sse41.c | 415 out[0] = loadu(&inputs[0][block_offset + 0 * sizeof(__m128i)]); in transpose_msg_vecs() 416 out[1] = loadu(&inputs[1][block_offset + 0 * sizeof(__m128i)]); in transpose_msg_vecs() 417 out[2] = loadu(&inputs[2][block_offset + 0 * sizeof(__m128i)]); in transpose_msg_vecs() 418 out[3] = loadu(&inputs[3][block_offset + 0 * sizeof(__m128i)]); in transpose_msg_vecs() 419 out[4] = loadu(&inputs[0][block_offset + 1 * sizeof(__m128i)]); in transpose_msg_vecs() 420 out[5] = loadu(&inputs[1][block_offset + 1 * sizeof(__m128i)]); in transpose_msg_vecs() 421 out[6] = loadu(&inputs[2][block_offset + 1 * sizeof(__m128i)]); in transpose_msg_vecs() 422 out[7] = loadu(&inputs[3][block_offset + 1 * sizeof(__m128i)]); in transpose_msg_vecs() 423 out[8] = loadu(&inputs[0][block_offset + 2 * sizeof(__m128i)]); in transpose_msg_vecs() 424 out[9] = loadu(&inputs[1][block_offset + 2 * sizeof(__m128i)]); in transpose_msg_vecs() [all …]
|
H A D | blake3_sse2.c | 421 out[0] = loadu(&inputs[0][block_offset + 0 * sizeof(__m128i)]); in transpose_msg_vecs() 422 out[1] = loadu(&inputs[1][block_offset + 0 * sizeof(__m128i)]); in transpose_msg_vecs() 423 out[2] = loadu(&inputs[2][block_offset + 0 * sizeof(__m128i)]); in transpose_msg_vecs() 424 out[3] = loadu(&inputs[3][block_offset + 0 * sizeof(__m128i)]); in transpose_msg_vecs() 425 out[4] = loadu(&inputs[0][block_offset + 1 * sizeof(__m128i)]); in transpose_msg_vecs() 426 out[5] = loadu(&inputs[1][block_offset + 1 * sizeof(__m128i)]); in transpose_msg_vecs() 427 out[6] = loadu(&inputs[2][block_offset + 1 * sizeof(__m128i)]); in transpose_msg_vecs() 428 out[7] = loadu(&inputs[3][block_offset + 1 * sizeof(__m128i)]); in transpose_msg_vecs() 429 out[8] = loadu(&inputs[0][block_offset + 2 * sizeof(__m128i)]); in transpose_msg_vecs() 430 out[9] = loadu(&inputs[1][block_offset + 2 * sizeof(__m128i)]); in transpose_msg_vecs() [all …]
|
/openbsd/sys/dev/pci/drm/radeon/ |
H A D | dce6_afmt.c | 34 u32 block_offset, u32 reg) in dce6_endpoint_rreg() argument 40 WREG32(AZ_F0_CODEC_ENDPOINT_INDEX + block_offset, reg); in dce6_endpoint_rreg() 41 r = RREG32(AZ_F0_CODEC_ENDPOINT_DATA + block_offset); in dce6_endpoint_rreg() 48 u32 block_offset, u32 reg, u32 v) in dce6_endpoint_wreg() argument 54 WREG32(AZ_F0_CODEC_ENDPOINT_INDEX + block_offset, reg); in dce6_endpoint_wreg() 56 WREG32(AZ_F0_CODEC_ENDPOINT_INDEX + block_offset, in dce6_endpoint_wreg() 58 WREG32(AZ_F0_CODEC_ENDPOINT_DATA + block_offset, v); in dce6_endpoint_wreg()
|
/openbsd/gnu/usr.bin/perl/cpan/IO-Compress/lib/IO/Uncompress/ |
H A D | RawInflate.pm | 307 my $block_offset = $headerLength + *$self->{Uncomp}->getLastBlockOffset(); 312 ( $self->smartSeek($block_offset) && 320 ( $self->smartSeek($block_offset) &&
|
/openbsd/gnu/llvm/lldb/source/Plugins/SymbolFile/DWARF/ |
H A D | DWARFDebugInfoEntry.cpp | 350 uint32_t block_offset = in GetDIENamesAndRanges() local 356 data, block_offset, block_length)), in GetDIENamesAndRanges()
|
H A D | SymbolFileDWARF.cpp | 3376 uint32_t block_offset = location_form.BlockData() - data.GetDataStart(); in ParseVariableDIE() local 3379 module, DataExtractor(data, block_offset, block_length), die.GetCU()); in ParseVariableDIE() 3400 uint32_t block_offset = in ParseVariableDIE() local 3404 module, DataExtractor(debug_info_data, block_offset, block_length), in ParseVariableDIE() 3921 uint32_t block_offset = form_value.BlockData() - data.GetDataStart(); in CollectCallSiteParameters() local 3924 module, DataExtractor(data, block_offset, block_length), in CollectCallSiteParameters() 4029 uint32_t block_offset = form_value.BlockData() - data.GetDataStart(); in CollectCallEdges() local 4032 module, DataExtractor(data, block_offset, block_length), in CollectCallEdges()
|
H A D | DWARFASTParserClang.cpp | 1406 uint32_t block_offset = in ParseInheritance() local 1410 DataExtractor(debug_info_data, block_offset, block_length), in ParseInheritance() 2526 uint32_t block_offset = in MemberAttributes() local 2532 DataExtractor(debug_info_data, block_offset, block_length), in MemberAttributes()
|
/openbsd/sys/dev/pci/drm/amd/amdgpu/ |
H A D | dce_v6_0.c | 128 u32 block_offset, u32 reg) in dce_v6_0_audio_endpt_rreg() argument 134 WREG32(mmAZALIA_F0_CODEC_ENDPOINT_INDEX + block_offset, reg); in dce_v6_0_audio_endpt_rreg() 135 r = RREG32(mmAZALIA_F0_CODEC_ENDPOINT_DATA + block_offset); in dce_v6_0_audio_endpt_rreg() 142 u32 block_offset, u32 reg, u32 v) in dce_v6_0_audio_endpt_wreg() argument 147 WREG32(mmAZALIA_F0_CODEC_ENDPOINT_INDEX + block_offset, in dce_v6_0_audio_endpt_wreg() 149 WREG32(mmAZALIA_F0_CODEC_ENDPOINT_DATA + block_offset, v); in dce_v6_0_audio_endpt_wreg()
|
H A D | dce_v8_0.c | 123 u32 block_offset, u32 reg) in dce_v8_0_audio_endpt_rreg() argument 129 WREG32(mmAZALIA_F0_CODEC_ENDPOINT_INDEX + block_offset, reg); in dce_v8_0_audio_endpt_rreg() 130 r = RREG32(mmAZALIA_F0_CODEC_ENDPOINT_DATA + block_offset); in dce_v8_0_audio_endpt_rreg() 137 u32 block_offset, u32 reg, u32 v) in dce_v8_0_audio_endpt_wreg() argument 142 WREG32(mmAZALIA_F0_CODEC_ENDPOINT_INDEX + block_offset, reg); in dce_v8_0_audio_endpt_wreg() 143 WREG32(mmAZALIA_F0_CODEC_ENDPOINT_DATA + block_offset, v); in dce_v8_0_audio_endpt_wreg()
|
H A D | dce_v10_0.c | 171 u32 block_offset, u32 reg) in dce_v10_0_audio_endpt_rreg() argument 177 WREG32(mmAZALIA_F0_CODEC_ENDPOINT_INDEX + block_offset, reg); in dce_v10_0_audio_endpt_rreg() 178 r = RREG32(mmAZALIA_F0_CODEC_ENDPOINT_DATA + block_offset); in dce_v10_0_audio_endpt_rreg() 185 u32 block_offset, u32 reg, u32 v) in dce_v10_0_audio_endpt_wreg() argument 190 WREG32(mmAZALIA_F0_CODEC_ENDPOINT_INDEX + block_offset, reg); in dce_v10_0_audio_endpt_wreg() 191 WREG32(mmAZALIA_F0_CODEC_ENDPOINT_DATA + block_offset, v); in dce_v10_0_audio_endpt_wreg()
|
H A D | dce_v11_0.c | 195 u32 block_offset, u32 reg) in dce_v11_0_audio_endpt_rreg() argument 201 WREG32(mmAZALIA_F0_CODEC_ENDPOINT_INDEX + block_offset, reg); in dce_v11_0_audio_endpt_rreg() 202 r = RREG32(mmAZALIA_F0_CODEC_ENDPOINT_DATA + block_offset); in dce_v11_0_audio_endpt_rreg() 209 u32 block_offset, u32 reg, u32 v) in dce_v11_0_audio_endpt_wreg() argument 214 WREG32(mmAZALIA_F0_CODEC_ENDPOINT_INDEX + block_offset, reg); in dce_v11_0_audio_endpt_wreg() 215 WREG32(mmAZALIA_F0_CODEC_ENDPOINT_DATA + block_offset, v); in dce_v11_0_audio_endpt_wreg()
|
/openbsd/gnu/usr.bin/binutils-2.17/bfd/ |
H A D | elf32-xtensa.c | 5590 bfd_vma block_offset, in insn_block_decodable_len() argument 5593 bfd_vma offset = block_offset; in insn_block_decodable_len() 5595 while (offset < block_offset + block_len) in insn_block_decodable_len() 5601 return (offset - block_offset); in insn_block_decodable_len() 5604 return (offset - block_offset); in insn_block_decodable_len()
|