Home
last modified time | relevance | path

Searched +full:3 +full:p0 (Results 1 – 25 of 309) sorted by relevance

12345678910>>...13

/freebsd/crypto/openssl/crypto/aes/asm/
H A Daes-ia64.S72 #define TE1 3
76 #define TE3 3
104 add te3=-3,te3 };;
120 { .mmi; (p0) LDKEY t0=[rk0],2*KSZ // 0/0:rk[0]
121 (p0) and te33=s3,maskff // 0/0:s3&0xff
122 (p0) extr.u te22=s2,8,8 } // 0/0:s2>>8&0xff
123 { .mmi; (p0) LDKEY t1=[rk1],2*KSZ // 0/1:rk[1]
124 (p0) and te30=s0,maskff // 0/1:s0&0xff
125 (p0) shr.u te00=s0,twenty4 };; // 0/0:s0>>24
126 { .mmi; (p0) LDKEY t2=[rk0],2*KSZ // 1/2:rk[2]
[all …]
/freebsd/contrib/libarchive/tar/test/
H A Dtest_option_r.c15 char *p0, *p1; in DEFINE_TEST() local
21 p0 = NULL; in DEFINE_TEST()
33 p0 = slurpfile(&s, "archive.tar"); in DEFINE_TEST()
34 if (!assert(p0 != NULL)) in DEFINE_TEST()
38 assertEqualMem(p0 + 0, "f1", 3); in DEFINE_TEST()
39 assertEqualMem(p0 + 512, "abc", 3); in DEFINE_TEST()
40 assertEqualMem(p0 + 1024, "\0\0\0\0\0\0\0\0", 8); in DEFINE_TEST()
41 assertEqualMem(p0 + 1536, "\0\0\0\0\0\0\0\0", 8); in DEFINE_TEST()
66 assertEqualMem(p0, p1, 1024); in DEFINE_TEST()
68 assertEqualMem(p1 + 1024, "f1", 3); in DEFINE_TEST()
[all …]
H A Dtest_option_C_mtree.c14 char *p0; in DEFINE_TEST() local
17 p0 = NULL; in DEFINE_TEST()
56 p0 = slurpfile(&s, "output.tar"); in DEFINE_TEST()
57 if (!assert(p0 != NULL)) in DEFINE_TEST()
61 assertEqualMem(p0 + 0, "./foo", 5); in DEFINE_TEST()
62 assertEqualMem(p0 + 512, "abc", 3); in DEFINE_TEST()
63 assertEqualMem(p0 + 1024, "\0\0\0\0\0\0\0\0", 8); in DEFINE_TEST()
64 assertEqualMem(p0 + 1536, "\0\0\0\0\0\0\0\0", 8); in DEFINE_TEST()
66 free(p0); in DEFINE_TEST()
/freebsd/sys/dev/adlink/
H A Dadlink.c2 * SPDX-License-Identifier: BSD-3-Clause
15 * 3. The names of the authors may not be used to endorse or promote
105 struct resource *res[3];
109 struct page0 *p0; member
141 sc->sample += sc->p0->chunksize / 2; in adlink_intr()
147 sc->p0->state = EIO; in adlink_intr()
149 if (sc->p0->state != STATE_RUN) { in adlink_intr()
150 printf("adlink: stopping %d\n", sc->p0->state); in adlink_intr()
158 bus_write_4(sc->res[0], 0x28, sc->p0->chunksize); in adlink_intr()
176 *paddr = vtophys(sc->p0); in adlink_mmap()
[all …]
/freebsd/contrib/diff/src/
H A Dio.c453 if (PTRDIFF_MAX / 3 <= alloc_lines in find_and_hash_each_line()
479 if (PTRDIFF_MAX / 3 <= alloc_lines in find_and_hash_each_line()
573 char *p0, *p1, *buffer0, *buffer1; in find_identical_ends() local
601 p0 = buffer0 = (char *) w0; in find_identical_ends()
606 if (p0 == p1) in find_identical_ends()
608 p0 = p1 += n1; in find_identical_ends()
615 p0[n0] = ~p1[n0]; in find_identical_ends()
617 p1[n1] = ~p0[n1]; in find_identical_ends()
626 p0 = (char *) w0; in find_identical_ends()
628 while (*p0 == *p1) in find_identical_ends()
[all …]
/freebsd/contrib/llvm-project/compiler-rt/lib/builtins/hexagon/
H A Ddfmul.S68 p0 = dfclass(A,#2) define
69 p0 = dfclass(B,#2) define
84 // Adding 2 HLs, we get 2^64-3*2^32+2 maximum.
85 // Therefore, we can add 3 2^32-1 values safely without carry. We only need one.
97 if (!p0) jump .Lmul_abnormal
124 p0 = !cmp.gt(EXP0,BTMPH) define
125 p0 = cmp.gt(EXP0,BTMPL) define
126 if (!p0.new) jump:nt .Lmul_ovf_unf
149 p0 = cmp.eq(AL,#0) define
150 p0 = bitsclr(AH,BTMPL) define
[all …]
H A Ddffma.S58 #define P_TMP p0
72 #define FUDGE2 3
119 ATMP = insert(A,#MANTBITS,#EXPBITS-3)
120 BTMP = insert(B,#MANTBITS,#EXPBITS-3)
139 CTMP = insert(C,#MANTBITS,#EXPBITS-3)
333 p0 = cmp.eq(TMP,#2) define
334 if (p0.new) AH = ##0x80000000
347 p0 = cmp.gtu(ONE,CTMP) define
348 if (p0.new) jump:nt .Ladd_yields_zero
385 p0 = cmp.gt(EXPA,##BIAS+BIAS) define
[all …]
H A Dmemcpy_likely_aligned.S24 p0 = bitsclr(r1,#7) define
25 p0 = bitsclr(r0,#7) define
26 if (p0.new) r5:4 = memd(r1)
27 r3 = #-3
30 if (!p0) jump .Lmemcpy_call
31 if (p0) memd(r0++#8) = r5:4
32 if (p0) r5:4 = memd(r1+#8)
33 r3 += lsr(r2,#3)
/freebsd/contrib/llvm-project/llvm/lib/Target/AArch64/GISel/
H A DAArch64LegalizerInfo.cpp46 const LLT p0 = LLT::pointer(0, 64); in AArch64LegalizerInfo() local
62 const LLT v2p0 = LLT::fixed_vector(2, p0); in AArch64LegalizerInfo()
75 std::initializer_list<LLT> ScalarAndPtrTypesList = {s8, s16, s32, s64, p0}; in AArch64LegalizerInfo()
97 .legalFor({p0, s8, s16, s32, s64}) in AArch64LegalizerInfo()
109 .legalFor({p0, s16, s32, s64}) in AArch64LegalizerInfo()
118 .clampMaxNumElements(0, p0, 2); in AArch64LegalizerInfo()
184 .legalFor({{p0, s64}, {v2p0, v2s64}}) in AArch64LegalizerInfo()
188 getActionDefinitionsBuilder(G_PTRMASK).legalFor({{p0, s64}}); in AArch64LegalizerInfo()
284 .legalIf(all(typeInSet(0, {s32, s64, p0}), in AArch64LegalizerInfo()
291 .maxScalarIf(typeInSet(0, {s64, p0}), 1, s32); in AArch64LegalizerInfo()
[all …]
/freebsd/contrib/llvm-project/clang/include/clang/Basic/
H A Darm_neon.td16 def OP_ADD : Op<(op "+", $p0, $p1)>;
17 def OP_ADDL : Op<(op "+", (call "vmovl", $p0), (call "vmovl", $p1))>;
18 def OP_ADDLHi : Op<(op "+", (call "vmovl_high", $p0),
20 def OP_ADDW : Op<(op "+", $p0, (call "vmovl", $p1))>;
21 def OP_ADDWHi : Op<(op "+", $p0, (call "vmovl_high", $p1))>;
22 def OP_SUB : Op<(op "-", $p0, $p1)>;
23 def OP_SUBL : Op<(op "-", (call "vmovl", $p0), (call "vmovl", $p1))>;
24 def OP_SUBLHi : Op<(op "-", (call "vmovl_high", $p0),
26 def OP_SUBW : Op<(op "-", $p0, (call "vmovl", $p1))>;
27 def OP_SUBWHi : Op<(op "-", $p0, (call "vmovl_high", $p1))>;
[all …]
H A Darm_neon_incl.td48 // $p0, the first $p1 etc.
52 // example: (op "+", $p0, $p1) -> "__p0 + __p1".
53 // (op "-", $p0) -> "-__p0"
60 // example: (call "vget_high", $p0) -> "vgetq_high_s16(__p0)"
61 // (assuming $p0 has type int16x8_t).
67 // example: (call_mangled "vfma_lane", $p0, $p1) -> "vfma_lane(__p0, __p1)"
69 // (call_mangled "vfma_lane", $p0, $p1) -> "vfma_laneq(__p0, __p1)"
81 // (cast $p0, $p1) would cast $p1 to the type of $p0.
84 // for example: (cast "uint32x4_t", $p0).
92 // example: (cast "R", "U", $p0) -> "(uint32x4_t)__p0" (assuming the return
[all …]
/freebsd/crypto/openssl/crypto/bn/asm/
H A Dia64.S185 cmp4.le p6,p0=r35,r0 };;
207 (p19) cmp.ltu.unc p56,p0=r40,r38 }
208 { .mfb; (p0) nop.m 0x0
209 (p0) nop.f 0x0
210 (p0) nop.b 0x0 }
212 (p58) cmp.eq.or p57,p0=-1,r41 // (p20)
215 (p0) nop.f 0x0
238 cmp4.le p6,p0=r35,r0 };;
260 (p19) cmp.gtu.unc p56,p0=r40,r38 }
261 { .mfb; (p0) nop.m 0x0
[all …]
/freebsd/contrib/llvm-project/clang/lib/Headers/
H A D__clang_cuda_texture_intrinsics.h76 : (s[3] == 0) ? 3 in __tex_len()
303 "{%0, %1, %2, %3}, [%4, {%5}];", ("f"(__x)));
305 "s32", "{%0, %1, %2, %3}, [%4, {%5}];", ("r"(__x)));
311 "{%0, %1, %2, %3}, [%4, {%5}], {%6}, {%7};",
317 "{%0, %1, %2, %3}, [%4, {%5, %6}];", ("r"(__layer), "f"(__x)));
323 "{%0, %1, %2, %3}, [%4, {%5, %6}], {%7}, {%8};",
329 "{%0, %1, %2, %3}, [%4, {%5, %6}], %7;",
334 "tex.level.1d.v4", "f32", "{%0, %1, %2, %3}, [%4, {%5}], %6;",
340 "f32", "{%0, %1, %2, %3}, [%4, {%5, %6}];", ("f"(__x), "f"(__y)));
344 "{.reg .pred %%p0;\n\t"
[all …]
/freebsd/crypto/openssl/crypto/rc2/
H A Drc2_cbc.c97 register RC2_INT *p0, *p1; in RC2_encrypt() local
108 n = 3; in RC2_encrypt()
111 p0 = p1 = &(key->data[0]); in RC2_encrypt()
113 t = (x0 + (x1 & ~x3) + (x2 & x3) + *(p0++)) & 0xffff; in RC2_encrypt()
115 t = (x1 + (x2 & ~x0) + (x3 & x0) + *(p0++)) & 0xffff; in RC2_encrypt()
117 t = (x2 + (x3 & ~x1) + (x0 & x1) + *(p0++)) & 0xffff; in RC2_encrypt()
118 x2 = (t << 3) | (t >> 13); in RC2_encrypt()
119 t = (x3 + (x0 & ~x2) + (x1 & x2) + *(p0++)) & 0xffff; in RC2_encrypt()
143 register RC2_INT *p0, *p1; in RC2_decrypt() local
154 n = 3; in RC2_decrypt()
[all …]
/freebsd/sys/contrib/openzfs/module/icp/algs/edonr/
H A Dedonr.c121 uint64_t p0, p1, p2, p3, p4, p5, p6, p7; in Q512() local
134 s64(3); in Q512()
153 LS2_512(d(0), d(1), d(2), d(3), d(4), d(5), d(6), d(7)); in Q512()
154 QEF_512(p0, p1, p2, p3, p4, p5, p6, p7); in Q512()
156 LS1_512(p0, p1, p2, p3, p4, p5, p6, p7); in Q512()
162 LS2_512(p0, p1, p2, p3, p4, p5, p6, p7); in Q512()
163 QEF_512(p0, p1, p2, p3, p4, p5, p6, p7); in Q512()
165 LS1_512(p0, p1, p2, p3, p4, p5, p6, p7); in Q512()
170 LS1_512(p0, p1, p2, p3, p4, p5, p6, p7); in Q512()
171 LS2_512(p[0], p[1], p[2], p[3], p[4], p[5], p[6], p[7]); in Q512()
[all …]
/freebsd/contrib/libarchive/libarchive/
H A Darchive_endian.h68 unsigned int p0 = p[0]; in archive_be16dec()
70 return ((p0 << 8) | p1); in archive_be16dec() local
81 unsigned int p3 = p[3]; in archive_be32dec()
84 unsigned int p0 = p[0]; in archive_be32dec()
86 return ((p0 << 24) | (p1 << 16) | (p2 << 8) | p3); in archive_be32dec() local
106 unsigned int p0 = p[0]; in archive_le16dec()
108 return ((p1 << 8) | p0); in archive_le16dec() local
119 unsigned int p3 = p[3]; in archive_le32dec()
122 unsigned int p0 = p[0]; in archive_le32dec()
124 return ((p3 << 24) | (p2 << 16) | (p1 << 8) | p0); in archive_le32dec() local
[all...]
/freebsd/contrib/llvm-project/llvm/lib/Target/Hexagon/MCTargetDesc/
H A DHexagonMCDuplexInfo.cpp233 // Rdd = memd(r29+#u5:3) in getDuplexCandidateGroup()
235 // [if ([!]p0[.new])] dealloc_return in getDuplexCandidateGroup()
236 // [if ([!]p0[.new])] jumpr r31 in getDuplexCandidateGroup()
244 inRange<3, 1>(MCI, 2)) { in getDuplexCandidateGroup()
254 inRange<3>(MCI, 2)) { in getDuplexCandidateGroup()
259 // Rdd = memd(r29+#u5:3) in getDuplexCandidateGroup()
264 inRange<5, 3>(MCI, 2)) { in getDuplexCandidateGroup()
295 // [if ([!]p0[.new])] jumpr r31 in getDuplexCandidateGroup()
296 if ((Hexagon::P0 == SrcReg) && (Hexagon::R31 == DstReg)) { in getDuplexCandidateGroup()
304 // [if ([!]p0[.new])] dealloc_return in getDuplexCandidateGroup()
[all …]
/freebsd/sys/contrib/openzfs/module/icp/algs/skein/
H A Dskein_block.c53 #define KW_KEY_BASE (3)
97 Xptr[3] = &X3; in Skein_256_Process_Block()
113 ks[3] = ctx->X[3]; in Skein_256_Process_Block()
114 ks[4] = ks[0] ^ ks[1] ^ ks[2] ^ ks[3] ^ SKEIN_KS_PARITY; in Skein_256_Process_Block()
126 X3 = w[3] + ks[3]; in Skein_256_Process_Block()
135 #define Round256(p0, p1, p2, p3, ROT, rNum) \ in Skein_256_Process_Block() argument
136 X##p0 += X##p1; X##p1 = RotL_64(X##p1, ROT##_0); X##p1 ^= X##p0; \ in Skein_256_Process_Block()
140 #define R256(p0, p1, p2, p3, ROT, rNum) /* fully unrolled */ \ in Skein_256_Process_Block() argument
141 Round256(p0, p1, p2, p3, ROT, rNum) \ in Skein_256_Process_Block()
146 X1 += ks[((R) + 2) % 5] + ts[((R) + 1) % 3]; \ in Skein_256_Process_Block()
[all …]
/freebsd/sys/crypto/skein/
H A Dskein_block.c39 #define KW_KEY_BASE (3)
85 Xptr[0] = &X0; Xptr[1] = &X1; Xptr[2] = &X2; Xptr[3] = &X3; in Skein_256_Process_Block()
98 ks[3] = ctx->X[3]; in Skein_256_Process_Block()
99 ks[4] = ks[0] ^ ks[1] ^ ks[2] ^ ks[3] ^ SKEIN_KS_PARITY; in Skein_256_Process_Block()
110 X3 = w[3] + ks[3]; in Skein_256_Process_Block()
118 #define Round256(p0,p1,p2,p3,ROT,rNum) \ in Skein_256_Process_Block() argument
119 X##p0 += X##p1; X##p1 = RotL_64(X##p1,ROT##_0); X##p1 ^= X##p0; \ in Skein_256_Process_Block()
123 #define R256(p0,p1,p2,p3,ROT,rNum) /* fully unrolled */ \ in Skein_256_Process_Block() argument
124 Round256(p0,p1,p2,p3,ROT,rNum) \ in Skein_256_Process_Block()
129 X1 += ks[((R)+2) % 5] + ts[((R)+1) % 3]; \ in Skein_256_Process_Block()
[all …]
/freebsd/contrib/llvm-project/llvm/lib/Target/Hexagon/
H A DHexagonDepMask.h358 /*p0=cmp.eq(Rs16,Rt16); if (!p0.new) jump:nt #r9:2*/
364 /*p0=cmp.eq(Rs16,Rt16); if (!p0.new) jump:t #r9:2*/
394 /*p0=cmp.eq(Rs16,Rt16); if (p0.new) jump:nt #r9:2*/
400 /*p0=cmp.eq(Rs16,Rt16); if (p0.new) jump:t #r9:2*/
430 /*p0=cmp.eq(Rs16,#U5); if (!p0.new) jump:nt #r9:2*/
436 /*p0=cmp.eq(Rs16,#U5); if (!p0.new) jump:t #r9:2*/
466 /*p0=cmp.eq(Rs16,#U5); if (p0.new) jump:nt #r9:2*/
472 /*p0=cmp.eq(Rs16,#U5); if (p0.new) jump:t #r9:2*/
502 /*p0=cmp.eq(Rs16,#-1); if (!p0.new) jump:nt #r9:2*/
508 /*p0=cmp.eq(Rs16,#-1); if (!p0.new) jump:t #r9:2*/
[all …]
/freebsd/crypto/openssl/crypto/poly1305/asm/
H A Dpoly1305-ia64.S15 // >3x faster. Originally it was argued that floating-point base 2^32
59 ADDP r11=3,r33 };;
149 cmp.eq p9,p0=1,r29
150 cmp.eq p10,p0=2,r29 }
151 { .mmi; cmp.eq p11,p0=3,r29
152 cmp.eq p12,p0=4,r29
153 cmp.eq p13,p0=5,r29 }
154 { .mmi; cmp.eq p14,p0=6,r29
155 cmp.eq p15,p0=7,r29
192 cmp.ltu p6,p0=h0,i0
[all …]
/freebsd/contrib/netbsd-tests/lib/libc/string/
H A Dt_memmem.c38 char p0[] = ""; variable
43 int lp2 = 3;
45 int lp3 = 3;
47 int lp4 = 3;
53 int lp7 = 3;
81 expect(memmem(b2, lb2, p0, lp0) == NULL); in ATF_TC_BODY()
82 expect(memmem(b0, lb0, p0, lp0) == NULL); in ATF_TC_BODY()
84 expect(memmem(b2, lb2, p0, lp0) == b2); in ATF_TC_BODY()
85 expect(memmem(b0, lb0, p0, lp0) == b0); in ATF_TC_BODY()
/freebsd/contrib/llvm-project/llvm/lib/Target/Mips/
H A DMipsLegalizerInfo.cpp80 const LLT p0 = LLT::pointer(0, 32); in MipsLegalizerInfo() local
109 Query, {{s32, p0, 8, NoAlignRequirements}, in MipsLegalizerInfo()
110 {s32, p0, 16, ST.systemSupportsUnalignedAccess()}, in MipsLegalizerInfo()
111 {s32, p0, 32, NoAlignRequirements}, in MipsLegalizerInfo()
112 {p0, p0, 32, NoAlignRequirements}, in MipsLegalizerInfo()
113 {s64, p0, 64, ST.systemSupportsUnalignedAccess()}})) in MipsLegalizerInfo()
116 Query, {{v16s8, p0, 128, NoAlignRequirements}, in MipsLegalizerInfo()
117 {v8s16, p0, 128, NoAlignRequirements}, in MipsLegalizerInfo()
118 {v4s32, p0, 128, NoAlignRequirements}, in MipsLegalizerInfo()
119 {v2s64, p0, 128, NoAlignRequirements}})) in MipsLegalizerInfo()
[all …]
/freebsd/contrib/llvm-project/llvm/lib/Target/RISCV/GISel/
H A DRISCVLegalizerInfo.cpp73 const LLT p0 = LLT::pointer(0, XLen); in RISCVLegalizerInfo() local
230 ConstantActions.legalFor({s32, p0}); in RISCVLegalizerInfo()
238 .legalFor({s32, sXLen, p0}) in RISCVLegalizerInfo()
245 .legalFor({{sXLen, sXLen}, {sXLen, p0}}) in RISCVLegalizerInfo()
254 .legalFor({{s32, sXLen}, {p0, sXLen}}) in RISCVLegalizerInfo()
265 .legalForTypesWithMemDesc({{s32, p0, s8, 8}, in RISCVLegalizerInfo()
266 {s32, p0, s16, 16}, in RISCVLegalizerInfo()
267 {s32, p0, s32, 32}, in RISCVLegalizerInfo()
268 {p0, p0, sXLen, XLen}}); in RISCVLegalizerInfo()
271 .legalForTypesWithMemDesc({{s32, p0, s8, 8}, {s32, p0, s16, 16}}); in RISCVLegalizerInfo()
[all …]
/freebsd/crypto/heimdal/lib/gssapi/krb5/
H A Darcfour.c17 * 3. Neither the name of the Institute nor the names of its contributors
175 u_char k6_data[16], *p0, *p; in _gssapi_get_mic_arcfour() local
187 p0 = _gssapi_make_mech_header(message_token->value, in _gssapi_get_mic_arcfour()
190 p = p0; in _gssapi_get_mic_arcfour()
205 p0 + 16, 8, /* SGN_CKSUM */ in _gssapi_get_mic_arcfour()
206 p0, 8, /* TOK_ID, SGN_ALG, Filer */ in _gssapi_get_mic_arcfour()
216 p0 + 16, 8, /* SGN_CKSUM */ in _gssapi_get_mic_arcfour()
228 p = p0 + 8; /* SND_SEQ */ in _gssapi_get_mic_arcfour()
365 u_char Klocaldata[16], k6_data[16], *p, *p0; in _gssapi_wrap_arcfour() local
393 p0 = _gssapi_make_mech_header(output_message_buffer->value, in _gssapi_wrap_arcfour()
[all …]

12345678910>>...13