Home
last modified time | relevance | path

Searched refs:l1 (Results 1 – 25 of 111) sorted by relevance

12345

/f-stack/freebsd/contrib/libsodium/test/default/
H A Dmetamorphic.c18 size_t l1, l2; in mm_generichash() local
38 l1 = randombytes_uniform((uint32_t) mlen); in mm_generichash()
40 crypto_generichash_update(&st, m, l1); in mm_generichash()
42 crypto_generichash_update(&st, m + l1 + l2, mlen - l1 - l2); in mm_generichash()
64 size_t l1, l2; in mm_onetimeauth() local
80 crypto_onetimeauth_update(&st, m, l1); in mm_onetimeauth()
82 crypto_onetimeauth_update(&st, m + l1 + l2, mlen - l1 - l2); in mm_onetimeauth()
104 size_t l1, l2; in mm_hmacsha256() local
122 crypto_auth_hmacsha256_update(&st, m + l1 + l2, mlen - l1 - l2); in mm_hmacsha256()
144 size_t l1, l2; in mm_hmacsha512() local
[all …]
/f-stack/freebsd/mips/mips/
H A Dcpu.c194 cpuinfo->l1.ic_nsets = in mips_get_identity()
207 cpuinfo->l1.dc_nways = in mips_get_identity()
209 cpuinfo->l1.dc_nsets = in mips_get_identity()
219 cpuinfo->l1.dc_nsets = 1; in mips_get_identity()
223 cpuinfo->l1.dc_nsets = 2; in mips_get_identity()
241 cpuinfo->l1.ic_size = cpuinfo->l1.ic_linesize in mips_get_identity()
242 * cpuinfo->l1.ic_nsets * cpuinfo->l1.ic_nways; in mips_get_identity()
243 cpuinfo->l1.dc_size = cpuinfo->l1.dc_linesize in mips_get_identity()
244 * cpuinfo->l1.dc_nsets * cpuinfo->l1.dc_nways; in mips_get_identity()
396 cpuinfo.l1.ic_nsets, cpuinfo.l1.ic_linesize); in cpu_identify()
[all …]
H A Dcache_mipsNN.c123 …flush_multiple_lines_per_way = cpuinfo->l1.ic_nsets * cpuinfo->l1.ic_linesize * cpuinfo->l1.ic_lin… in mipsNN_cache_init()
135 picache_loopcount = (cpuinfo->l1.ic_nsets * cpuinfo->l1.ic_linesize / PAGE_SIZE) * in mipsNN_cache_init()
136 cpuinfo->l1.ic_nways; in mipsNN_cache_init()
138 picache_stride = cpuinfo->l1.ic_nsets * cpuinfo->l1.ic_linesize; in mipsNN_cache_init()
139 picache_loopcount = cpuinfo->l1.ic_nways; in mipsNN_cache_init()
142 if (cpuinfo->l1.dc_nsets * cpuinfo->l1.dc_linesize < PAGE_SIZE) { in mipsNN_cache_init()
143 pdcache_stride = cpuinfo->l1.dc_nsets * cpuinfo->l1.dc_linesize; in mipsNN_cache_init()
147 pdcache_loopcount = (cpuinfo->l1.dc_nsets * cpuinfo->l1.dc_linesize / PAGE_SIZE) * in mipsNN_cache_init()
148 cpuinfo->l1.dc_nways; in mipsNN_cache_init()
154 picache_size = cpuinfo->l1.ic_size; in mipsNN_cache_init()
[all …]
H A Dcache.c94 switch (cpuinfo->l1.ic_linesize) { in mips_config_cache()
133 cpuinfo->l1.ic_linesize); in mips_config_cache()
136 switch (cpuinfo->l1.dc_linesize) { in mips_config_cache()
228 cpuinfo->l1.dc_linesize); in mips_config_cache()
260 if (cpuinfo->l1.ic_size) { in mips_config_cache()
270 if (cpuinfo->l1.dc_size) { in mips_config_cache()
/f-stack/freebsd/contrib/openzfs/lib/libspl/
H A Dstrlcat.c43 size_t l1; in strlcat() local
49 l1 = df - dst; in strlcat()
50 if (dstsize == l1) in strlcat()
51 return (l1 + l2); in strlcat()
53 copied = l1 + l2 >= dstsize ? dstsize - l1 - 1 : l2; in strlcat()
54 (void) memcpy(dst + l1, src, copied); in strlcat()
55 dst[l1+copied] = '\0'; in strlcat()
57 return (l1 + l2); in strlcat()
/f-stack/app/redis-5.0.5/src/
H A Dmemtest.c148 l1 = l+off; in memtest_fill_random()
149 l2 = l1+words; in memtest_fill_random()
153 l1 += step; in memtest_fill_random()
173 l1 = l+off; in memtest_fill_value()
174 l2 = l1+words; in memtest_fill_value()
186 l1 += step; in memtest_fill_value()
199 l1 = l; in memtest_compare()
200 l2 = l1+words; in memtest_compare()
202 if (*l1 != *l2) { in memtest_compare()
205 (void*)l1, (void*)l2, *l1, *l2); in memtest_compare()
[all …]
/f-stack/freebsd/contrib/device-tree/src/arm64/qcom/
H A Dsdm660.dtsi49 L1_I_100: l1-icache {
52 L1_D_100: l1-dcache {
64 L1_I_101: l1-icache {
113 L1_I_0: l1-icache {
116 L1_D_0: l1-dcache {
128 L1_I_1: l1-icache {
131 L1_D_1: l1-dcache {
143 L1_I_2: l1-icache {
146 L1_D_2: l1-dcache {
158 L1_I_3: l1-icache {
[all …]
H A Dmsm8998.dtsi142 L1_I_0: l1-icache {
145 L1_D_0: l1-dcache {
157 L1_I_1: l1-icache {
160 L1_D_1: l1-dcache {
172 L1_I_2: l1-icache {
175 L1_D_2: l1-dcache {
187 L1_I_3: l1-icache {
190 L1_D_3: l1-dcache {
206 L1_I_100: l1-icache {
209 L1_D_100: l1-dcache {
[all …]
/f-stack/freebsd/crypto/des/
H A Ddes_ecb.c120 register DES_LONG l0,l1; in des_ecb3_encrypt() local
126 c2l(in,l1); in des_ecb3_encrypt()
128 ll[1]=l1; in des_ecb3_encrypt()
136 l1=ll[1]; in des_ecb3_encrypt()
138 l2c(l1,out); in des_ecb3_encrypt()
H A Ddes_locl.h75 #define c2ln(c,l1,l2,n) { \ argument
77 l1=l2=0; \
83 case 4: l1 =((DES_LONG)(*(--(c))))<<24L; \
84 case 3: l1|=((DES_LONG)(*(--(c))))<<16L; \
85 case 2: l1|=((DES_LONG)(*(--(c))))<< 8L; \
86 case 1: l1|=((DES_LONG)(*(--(c)))); \
110 #define l2cn(l1,l2,c,n) { \ argument
117 case 4: *(--(c))=(unsigned char)(((l1)>>24L)&0xff); \
118 case 3: *(--(c))=(unsigned char)(((l1)>>16L)&0xff); \
119 case 2: *(--(c))=(unsigned char)(((l1)>> 8L)&0xff); \
[all …]
/f-stack/freebsd/arm64/arm64/
H A Defirt_machdep.c100 pd_entry_t *l0, *l1, *l2; in efi_1t1_l3() local
116 l1 = (pd_entry_t *)PHYS_TO_DMAP(mphys); in efi_1t1_l3()
118 l1 += l1_idx; in efi_1t1_l3()
119 if (*l1 == 0) { in efi_1t1_l3()
122 *l1 = mphys | L1_TABLE; in efi_1t1_l3()
124 mphys = *l1 & ~ATTR_MASK; in efi_1t1_l3()
H A Dpmap.c444 pd_entry_t *l1; in pmap_l0_to_l1() local
484 pd_entry_t *l1; in pmap_l2() local
540 return (l1); in pmap_pde()
566 return (l1); in pmap_pte()
617 *l1 = l1p; in pmap_get_tables()
750 pd_entry_t *l1; in pmap_early_page_idx() local
890 pd_entry_t *l1; in pmap_bootstrap_l2() local
1920 l1 = &l1[ptepindex & Ln_ADDR_MASK]; in _pmap_alloc_l3()
1942 l1 = &l1[l1index & Ln_ADDR_MASK]; in _pmap_alloc_l3()
1945 l1 = &l1[l1index & Ln_ADDR_MASK]; in _pmap_alloc_l3()
[all …]
H A Dminidump_machdep.c208 pd_entry_t *l0, *l1, *l2; in minidumpsys() local
222 if (!pmap_get_tables(pmap_kernel(), va, &l0, &l1, &l2, &l3)) in minidumpsys()
225 if ((*l1 & ATTR_DESCR_MASK) == L1_BLOCK) { in minidumpsys()
226 pa = *l1 & ~ATTR_MASK; in minidumpsys()
319 if (!pmap_get_tables(pmap_kernel(), va, &l0, &l1, &l2, &l3)) { in minidumpsys()
328 } else if ((*l1 & ATTR_DESCR_MASK) == L1_BLOCK) { in minidumpsys()
333 pa = (*l1 & ~ATTR_MASK) | (va & L1_OFFSET); in minidumpsys()
/f-stack/app/redis-5.0.5/deps/lua/src/
H A Dlstring.c79 size_t l1; in luaS_newlstr() local
80 for (l1=l; l1>=step; l1-=step) /* compute hash */ in luaS_newlstr()
81 h = h ^ ((h<<5)+(h>>2)+cast(unsigned char, str[l1-1])); in luaS_newlstr()
H A Dlstrlib.c444 static const char *lmemfind (const char *s1, size_t l1, in lmemfind() argument
447 else if (l2 > l1) return NULL; /* avoids a negative `l1' */ in lmemfind()
451 l1 = l1-l2; /* `s2' cannot be found after that */ in lmemfind()
452 while (l1 > 0 && (init = (const char *)memchr(s1, *s2, l1)) != NULL) { in lmemfind()
457 l1 -= init-s1; in lmemfind()
496 size_t l1, l2; in str_find_aux() local
497 const char *s = luaL_checklstring(L, 1, &l1); in str_find_aux()
499 ptrdiff_t init = posrelat(luaL_optinteger(L, 3, 1), l1) - 1; in str_find_aux()
501 else if ((size_t)(init) > l1) init = (ptrdiff_t)l1; in str_find_aux()
505 const char *s2 = lmemfind(s+init, l1-init, p, l2); in str_find_aux()
[all …]
/f-stack/dpdk/lib/librte_node/
H A Dpkt_cls.c38 uint8_t l0, l1, l2, l3, last_type; in pkt_cls_node_process() local
83 l1 = mbuf1->packet_type & in pkt_cls_node_process()
93 uint8_t fix_spec = (last_type ^ l0) | (last_type ^ l1) | in pkt_cls_node_process()
116 if (p_nxt[l1] == next_index) { in pkt_cls_node_process()
122 p_nxt[l1], from[1]); in pkt_cls_node_process()
/f-stack/freebsd/contrib/device-tree/Bindings/regulator/
H A Dqcom,smd-rpm-regulator.yaml29 For pm8916, s1, s2, s3, s4, l1, l2, l3, l4, l5, l6, l7, l8, l9, l10, l11,
32 For pm8941, s1, s2, s3, s4, l1, l2, l3, l4, l5, l6, l7, l8, l9, l10, l11,
36 For pm8994, s1, s2, s3, s4, s5, s6, s7, s8, s9, s10, s11, s12, l1, l2, l3,
40 For pm8998, s1, s2, s3, s4, s5, s6, s7, s8, s9, s10, s11, s12, s13, l1, l2,
44 For pma8084, s1, s2, s3, s4, s5, s6, s7, s8, s9, s10, s11, s12, l1, l2, l3,
52 For pms405, s1, s2, s3, s4, s5, l1, l2, l3, l4, l5, l6, l7, l8, l9, l10, l11,
H A Dqcom,spmi-regulator.txt174 s1, s2, s3, s4, l1, l2, l3, l4, l5, l6, l7, l8, l9, l10, l11, l12, l13,
178 s1, s2, s3, s4, l1, l2, l3, l4, l5, l6, l7, l8, l9, l10, l11, l12, l13,
183 s1, s2, s3, s4, s5, s6, s7, s8, s9, s10, s11, s12, l1, l2, l3, l4, l5,
188 s1, s2, s3, l1
280 l1: l1 {
H A Dqcom,smd-rpm-regulator.txt249 s1, s2, s3, s4, l1, l2, l3, l4, l5, l6, l7, l8, l9, l10, l11, l12, l13,
253 s1, s2, s3, s4, l1, l2, l3, l4, l5, l6, l7, l8, l9, l10, l11, l12, l13,
258 s1, s2, s3, s4, s5, s6, s7, s8, s9, s10, s11, s12, l1, l2, l3, l4, l5,
263 s1, s2, s3, s4, s5, s6, s7, s8, s9, s10, s11, s12, s13, l1, l2, l3, l4,
268 s1, s2, s3, s4, s5, s6, s7, s8, s9, s10, s11, s12, l1, l2, l3, l4, l5,
279 s1, s2, s3, s4, s5, l1, l2, l3, l4, l5, l6, l7, l8, l9, l10, l11, l12,
/f-stack/freebsd/contrib/device-tree/Bindings/interrupt-controller/
H A Dbrcm,bcm6345-l1-intc.txt26 - compatible: should be "brcm,bcm<soc>-l1-intc", "brcm,bcm6345-l1-intc"
46 compatible = "brcm,bcm63168-l1-intc", "brcm,bcm6345-l1-intc";
H A Dbrcm,bcm2836-l1-intc.txt10 - compatible: Should be "brcm,bcm2836-l1-intc"
32 compatible = "brcm,bcm2836-l1-intc";
/f-stack/freebsd/contrib/openzfs/module/lua/
H A Dlstring.c52 size_t l1; in luaS_hash() local
54 for (l1 = l; l1 >= step; l1 -= step) in luaS_hash()
55 h = h ^ ((h<<5) + (h>>2) + cast_byte(str[l1 - 1])); in luaS_hash()
/f-stack/dpdk/lib/librte_acl/
H A Dacl_run_avx2.h96 xmm_t l0, l1; in acl_process_matches_avx2x8() local
100 l1 = _mm256_extracti128_si256(*tr_lo, 1); in acl_process_matches_avx2x8()
110 tr[i + 4] = (uint32_t)_mm_cvtsi128_si32(l1); in acl_process_matches_avx2x8()
113 l1 = _mm_srli_si128(l1, sizeof(uint32_t)); in acl_process_matches_avx2x8()
/f-stack/freebsd/amd64/include/
H A Dpmap.h169 #define KV4ADDR(l4, l3, l2, l1) ( \ argument
174 ((unsigned long)(l1) << PAGE_SHIFT))
175 #define KV5ADDR(l5, l4, l3, l2, l1) ( \ argument
181 ((unsigned long)(l1) << PAGE_SHIFT))
183 #define UVADDR(l5, l4, l3, l2, l1) ( \ argument
188 ((unsigned long)(l1) << PAGE_SHIFT))
/f-stack/freebsd/amd64/amd64/
H A Dlocore.S91 leaq l1(%rip),%rax
98 l1: movl $(3<<3),%eax label

12345