Home
last modified time | relevance | path

Searched refs:block_len (Results 1 – 25 of 32) sorted by relevance

12

/freebsd/sys/contrib/openzfs/module/icp/algs/blake3/
H A Dblake3_impl.c42 const uint8_t block[BLAKE3_BLOCK_LEN], uint8_t block_len,
46 const uint8_t block[BLAKE3_BLOCK_LEN], uint8_t block_len,
55 const uint8_t block[BLAKE3_BLOCK_LEN], uint8_t block_len, in blake3_compress_in_place_sse2() argument
58 zfs_blake3_compress_in_place_sse2(cv, block, block_len, counter, in blake3_compress_in_place_sse2()
64 const uint8_t block[BLAKE3_BLOCK_LEN], uint8_t block_len, in blake3_compress_xof_sse2() argument
67 zfs_blake3_compress_xof_sse2(cv, block, block_len, counter, flags, in blake3_compress_xof_sse2()
106 const uint8_t block[BLAKE3_BLOCK_LEN], uint8_t block_len,
110 const uint8_t block[BLAKE3_BLOCK_LEN], uint8_t block_len,
119 const uint8_t block[BLAKE3_BLOCK_LEN], uint8_t block_len, in blake3_compress_in_place_sse41() argument
122 zfs_blake3_compress_in_place_sse41(cv, block, block_len, counter, in blake3_compress_in_place_sse41()
[all …]
H A Dblake3_generic.c67 const uint8_t block[BLAKE3_BLOCK_LEN], uint8_t block_len, in compress_pre() argument
102 state[14] = (uint32_t)block_len; in compress_pre()
115 const uint8_t block[BLAKE3_BLOCK_LEN], uint8_t block_len, in blake3_compress_in_place_generic() argument
119 compress_pre(state, cv, block, block_len, counter, flags); in blake3_compress_in_place_generic()
151 const uint8_t block[BLAKE3_BLOCK_LEN], uint8_t block_len, in blake3_compress_xof_generic() argument
155 compress_pre(state, cv, block, block_len, counter, flags); in blake3_compress_xof_generic()
H A Dblake3.c48 uint8_t block_len; member
114 const uint8_t *block, uint8_t block_len, in make_output() argument
120 ret.block_len = block_len; in make_output()
139 ops->compress_in_place(cv_words, ctx->block, ctx->block_len, in output_chaining_value()
151 ops->compress_xof(ctx->input_cv, ctx->block, ctx->block_len, in output_root_bytes()
H A Dblake3_impl.h45 uint8_t block_len, uint64_t counter,
49 const uint8_t block[BLAKE3_BLOCK_LEN], uint8_t block_len,
/freebsd/contrib/llvm-project/llvm/lib/Support/BLAKE3/
H A Dblake3_dispatch.c171 uint8_t block_len, uint64_t counter, in blake3_compress_in_place() argument
178 blake3_compress_in_place_avx512(cv, block, block_len, counter, flags); in blake3_compress_in_place()
184 blake3_compress_in_place_sse41(cv, block, block_len, counter, flags); in blake3_compress_in_place()
190 blake3_compress_in_place_sse2(cv, block, block_len, counter, flags); in blake3_compress_in_place()
195 blake3_compress_in_place_portable(cv, block, block_len, counter, flags); in blake3_compress_in_place()
200 uint8_t block_len, uint64_t counter, uint8_t flags, in blake3_compress_xof() argument
207 blake3_compress_xof_avx512(cv, block, block_len, counter, flags, out); in blake3_compress_xof()
213 blake3_compress_xof_sse41(cv, block, block_len, counter, flags, out); in blake3_compress_xof()
219 blake3_compress_xof_sse2(cv, block, block_len, counter, flags, out); in blake3_compress_xof()
224 blake3_compress_xof_portable(cv, block, block_len, counter, flags, out); in blake3_compress_xof()
[all …]
H A Dblake3_impl.h201 uint8_t block_len, uint64_t counter,
207 uint8_t block_len, uint64_t counter, uint8_t flags,
213 uint8_t block_len, uint64_t counter, uint8_t flags,
246 uint8_t block_len, uint64_t counter,
252 uint8_t block_len, uint64_t counter,
267 uint8_t block_len, uint64_t counter,
272 uint8_t block_len, uint64_t counter,
285 uint8_t block_len, uint64_t counter,
290 uint8_t block_len, uint64_t counter,
311 uint8_t block_len, uint64_t counter,
[all …]
H A Dblake3_portable.c39 uint8_t block_len, uint64_t counter, uint8_t flags) { in compress_pre() argument
72 state[14] = (uint32_t)block_len; in compress_pre()
86 uint8_t block_len, uint64_t counter, in blake3_compress_in_place_portable() argument
89 compress_pre(state, cv, block, block_len, counter, flags); in blake3_compress_in_place_portable()
102 uint8_t block_len, uint64_t counter, in blake3_compress_xof_portable() argument
105 compress_pre(state, cv, block, block_len, counter, flags); in blake3_compress_xof_portable()
H A Dblake3.c65 uint8_t block_len; member
71 uint8_t block_len, uint64_t counter, in make_output() argument
76 ret.block_len = block_len; in make_output()
91 blake3_compress_in_place(cv_words, self->block, self->block_len, in output_chaining_value()
105 …blake3_compress_xof(self->input_cv, self->block, self->block_len, output_block_counter, self->flag… in output_root_bytes()
114 …blake3_xof_many(self->input_cv, self->block, self->block_len, output_block_counter, self->flags | … in output_root_bytes()
120 …blake3_compress_xof(self->input_cv, self->block, self->block_len, output_block_counter, self->flag… in output_root_bytes()
H A Dblake3_avx512.c122 uint8_t block_len, uint64_t counter, uint8_t flags) { in compress_pre() argument
127 (uint32_t)block_len, (uint32_t)flags); in compress_pre()
293 uint8_t block_len, uint64_t counter, in blake3_compress_xof_avx512() argument
296 compress_pre(rows, cv, block, block_len, counter, flags); in blake3_compress_xof_avx512()
305 uint8_t block_len, uint64_t counter, in blake3_compress_in_place_avx512() argument
308 compress_pre(rows, cv, block, block_len, counter, flags); in blake3_compress_in_place_avx512()
560 uint8_t block_len, uint64_t counter, uint8_t flags, in blake3_xof4_avx512() argument
574 __m128i block_len_vec = set1_128(block_len); in blake3_xof4_avx512()
860 uint8_t block_len, uint64_t counter, uint8_t flags, in blake3_xof8_avx512() argument
874 __m256i block_len_vec = set1_256(block_len); in blake3_xof8_avx512()
[all …]
H A Dblake3_sse41.c85 uint8_t block_len, uint64_t counter, uint8_t flags) { in compress_pre() argument
90 (uint32_t)block_len, (uint32_t)flags); in compress_pre()
256 uint8_t block_len, uint64_t counter, in blake3_compress_in_place_sse41() argument
259 compress_pre(rows, cv, block, block_len, counter, flags); in blake3_compress_in_place_sse41()
266 uint8_t block_len, uint64_t counter, in blake3_compress_xof_sse41() argument
269 compress_pre(rows, cv, block, block_len, counter, flags); in blake3_compress_xof_sse41()
H A Dblake3_sse2.c91 uint8_t block_len, uint64_t counter, uint8_t flags) { in compress_pre() argument
96 (uint32_t)block_len, (uint32_t)flags); in compress_pre()
262 uint8_t block_len, uint64_t counter, in blake3_compress_in_place_sse2() argument
265 compress_pre(rows, cv, block, block_len, counter, flags); in blake3_compress_in_place_sse2()
272 uint8_t block_len, uint64_t counter, in blake3_compress_xof_sse2() argument
275 compress_pre(rows, cv, block, block_len, counter, flags); in blake3_compress_xof_sse2()
H A Dblake3_neon.c318 uint8_t block_len, uint64_t counter,
/freebsd/contrib/libucl/src/
H A Dmum.h342 size_t block_len; in _mum_hash_default() local
350 block_len = len < _MUM_BLOCK_LEN ? len : _MUM_BLOCK_LEN; in _mum_hash_default()
351 memmove(buf, str, block_len); in _mum_hash_default()
352 result = _mum_hash_aligned(result, buf, block_len); in _mum_hash_default()
353 len -= block_len; in _mum_hash_default()
354 str += block_len; in _mum_hash_default()
/freebsd/crypto/openssl/crypto/cmac/
H A Dcmac.c116 int block_len; in ossl_cmac_init() local
125 block_len = EVP_CIPHER_CTX_get_block_size(ctx->cctx); in ossl_cmac_init()
126 if (block_len == 0) in ossl_cmac_init()
128 memset(ctx->tbl, 0, block_len); in ossl_cmac_init()
/freebsd/contrib/llvm-project/lldb/source/Symbol/
H A DDWARFCallFrameInfo.cpp894 size_t block_len = (size_t)m_cfi_data.GetULEB128(&offset); in HandleCommonDwarfOpcode() local
896 static_cast<const uint8_t *>(m_cfi_data.GetData(&offset, block_len)); in HandleCommonDwarfOpcode()
897 row.GetCFAValue().SetIsDWARFExpression(block_data, block_len); in HandleCommonDwarfOpcode()
911 uint32_t block_len = (uint32_t)m_cfi_data.GetULEB128(&offset); in HandleCommonDwarfOpcode() local
913 static_cast<const uint8_t *>(m_cfi_data.GetData(&offset, block_len)); in HandleCommonDwarfOpcode()
915 reg_location.SetAtDWARFExpression(block_data, block_len); in HandleCommonDwarfOpcode()
967 uint32_t block_len = (uint32_t)m_cfi_data.GetULEB128(&offset); in HandleCommonDwarfOpcode() local
969 (const uint8_t *)m_cfi_data.GetData(&offset, block_len); in HandleCommonDwarfOpcode()
970 reg_location.SetIsDWARFExpression(block_data, block_len); in HandleCommonDwarfOpcode()
/freebsd/usr.sbin/camdd/
H A Dcamdd.c257 uint32_t block_len; member
289 uint32_t block_len; member
456 int probe_timeout, uint64_t *maxsector, uint32_t *block_len);
459 int probe_timeout, uint64_t *maxsector, uint32_t *block_len);
1285 int probe_timeout, uint64_t *maxsector, uint32_t *block_len) in camdd_probe_pass_scsi() argument
1327 *block_len = scsi_4btoul(rcap.length); in camdd_probe_pass_scsi()
1370 *block_len = scsi_4btoul(rcaplong.length); in camdd_probe_pass_scsi()
1381 int probe_timeout, uint64_t *maxsector, uint32_t *block_len) in camdd_probe_pass_nvme() argument
1435 *block_len = 1 << lbads; in camdd_probe_pass_nvme()
1458 uint32_t block_len = 0; in camdd_probe_pass() local
[all …]
/freebsd/contrib/llvm-project/llvm/lib/Support/
H A Dxxhash.cpp525 const size_t block_len = XXH_STRIPE_LEN * nbStripesPerBlock; in XXH3_hashLong_64b() local
526 const size_t nb_blocks = (len - 1) / block_len; in XXH3_hashLong_64b()
532 XXH3_accumulate(acc, input + n * block_len, secret, nbStripesPerBlock); in XXH3_hashLong_64b()
537 const size_t nbStripes = (len - 1 - (block_len * nb_blocks)) / XXH_STRIPE_LEN; in XXH3_hashLong_64b()
539 XXH3_accumulate(acc, input + nb_blocks * block_len, secret, nbStripes); in XXH3_hashLong_64b()
988 const size_t block_len = XXH_STRIPE_LEN * nbStripesPerBlock; in XXH3_hashLong_128b() local
989 const size_t nb_blocks = (len - 1) / block_len; in XXH3_hashLong_128b()
996 XXH3_accumulate(acc, input + n * block_len, secret, nbStripesPerBlock); in XXH3_hashLong_128b()
1001 const size_t nbStripes = (len - 1 - (block_len * nb_blocks)) / XXH_STRIPE_LEN; in XXH3_hashLong_128b()
1003 XXH3_accumulate(acc, input + nb_blocks * block_len, secret, nbStripes); in XXH3_hashLong_128b()
/freebsd/crypto/openssl/providers/implementations/macs/
H A Dkmac_prov.c312 size_t out_len, block_len; in kmac_init() local
335 block_len = t; in kmac_init()
347 kctx->custom, kctx->custom_len, block_len)) { in kmac_init()
355 kctx->custom, kctx->custom_len, block_len) in kmac_init()
/freebsd/crypto/openssh/
H A Ddigest-libc.c64 size_t block_len; member
169 return digest == NULL ? 0 : digest->block_len; in ssh_digest_blocksize()
/freebsd/sys/dev/xdma/
H A Dxdma_queue.c89 xr->block_len = len; in xdma_enqueue()
H A Dxdma.h112 bus_size_t block_len; member
H A Dxdma_fdt_test.c239 sc->req.block_len = sc->len; in xdmatest_test()
H A Dxdma_sg.c444 addr, (xr->block_len * xr->block_num), in _xdma_load_data_busdma()
/freebsd/contrib/unbound/sldns/
H A Dwire2str.c1596 unsigned i, bit, window, block_len; in sldns_wire2str_nsec_scan() local
1603 block_len = (unsigned)p[1]; in sldns_wire2str_nsec_scan()
1604 if(pl < 2+block_len) return -1; in sldns_wire2str_nsec_scan()
1605 p += block_len+2; in sldns_wire2str_nsec_scan()
1606 pl -= block_len+2; in sldns_wire2str_nsec_scan()
1615 block_len = (unsigned)p[1]; in sldns_wire2str_nsec_scan()
1616 if(pl < 2+block_len) return -1; /* cannot happen */ in sldns_wire2str_nsec_scan()
1618 for(i=0; i<block_len; i++) { in sldns_wire2str_nsec_scan()
1630 p += block_len; in sldns_wire2str_nsec_scan()
1631 pl -= block_len+2; in sldns_wire2str_nsec_scan()
/freebsd/sys/cam/scsi/
H A Dscsi_da.c1552 static void dasetgeom(struct cam_periph *periph, uint32_t block_len,
6408 dasetgeom(struct cam_periph *periph, uint32_t block_len, uint64_t maxsector, in dasetgeom() argument
6420 dp->secsize = block_len; in dasetgeom()
6438 dp->stripesize = block_len << lbppbe; in dasetgeom()
6439 dp->stripeoffset = (dp->stripesize - block_len * lalba) % in dasetgeom()
6445 dp->stripesize = block_len * softc->unmap_gran; in dasetgeom()
6446 dp->stripeoffset = (dp->stripesize - block_len * in dasetgeom()

12