Home
last modified time | relevance | path

Searched refs:src1 (Results 1 – 25 of 180) sorted by relevance

12345678

/freebsd/contrib/llvm-project/llvm/lib/Target/Hexagon/
H A DHexagonDepMapAsm2Intrin.td14 def: Pat<(int_hexagon_A2_abs IntRegs:$src1),
15 (A2_abs IntRegs:$src1)>, Requires<[HasV5]>;
16 def: Pat<(int_hexagon_A2_absp DoubleRegs:$src1),
17 (A2_absp DoubleRegs:$src1)>, Requires<[HasV5]>;
18 def: Pat<(int_hexagon_A2_abssat IntRegs:$src1),
19 (A2_abssat IntRegs:$src1)>, Requires<[HasV5]>;
20 def: Pat<(int_hexagon_A2_add IntRegs:$src1, IntRegs:$src2),
21 (A2_add IntRegs:$src1, IntRegs:$src2)>, Requires<[HasV5]>;
22 def: Pat<(int_hexagon_A2_addh_h16_hh IntRegs:$src1, IntRegs:$src2),
23 (A2_addh_h16_hh IntRegs:$src1, IntRegs:$src2)>, Requires<[HasV5]>;
[all …]
H A DHexagonMapAsm2IntrinV62.gen.td10 def: Pat<(IntID HvxVR:$src1, IntRegs:$src2),
11 (MI HvxVR:$src1, IntRegs:$src2)>;
12 def: Pat<(!cast<Intrinsic>(IntID#"_128B") HvxVR:$src1, IntRegs:$src2),
13 (MI HvxVR:$src1, IntRegs:$src2)>;
17 def: Pat<(IntID HvxVR:$src1, HvxVR:$src2, IntRegsLow8:$src3),
18 (MI HvxVR:$src1, HvxVR:$src2, IntRegsLow8:$src3)>;
19 def: Pat<(!cast<Intrinsic>(IntID#"_128B") HvxVR:$src1, HvxVR:$src2,
21 (MI HvxVR:$src1, HvxVR:$src2, IntRegsLow8:$src3)>;
25 def: Pat<(IntID HvxVR:$src1, HvxVR:$src2),
26 (MI HvxVR:$src1, HvxVR:$src2)>;
[all …]
H A DHexagonIntrinsicsV60.td15 def : Pat < (v16i32 (int_hexagon_V6_lo (v32i32 HvxWR:$src1))),
16 (v16i32 (EXTRACT_SUBREG (v32i32 HvxWR:$src1), vsub_lo)) >;
18 def : Pat < (v16i32 (int_hexagon_V6_hi (v32i32 HvxWR:$src1))),
19 (v16i32 (EXTRACT_SUBREG (v32i32 HvxWR:$src1), vsub_hi)) >;
21 def : Pat < (v32i32 (int_hexagon_V6_lo_128B (v64i32 HvxWR:$src1))),
22 (v32i32 (EXTRACT_SUBREG (v64i32 HvxWR:$src1), vsub_lo)) >;
24 def : Pat < (v32i32 (int_hexagon_V6_hi_128B (v64i32 HvxWR:$src1))),
25 (v32i32 (EXTRACT_SUBREG (v64i32 HvxWR:$src1), vsub_hi)) >;
28 def : Pat <(v64i1 (bitconvert (v16i32 HvxVR:$src1))),
29 (v64i1 (V6_vandvrt(v16i32 HvxVR:$src1), (A2_tfrsi 0x01010101)))>;
[all …]
/freebsd/contrib/sendmail/libsm/
H A Dt-strl.c31 char src1[N][SIZE], dst1[SIZE], dst2[SIZE]; variable
92 (void) sm_strlcpy(src1[k], "abcdef", sizeof src1);
95 one = sm_strlcpyn(dst1, sizeof dst1, 3, src1[0], "/", src1[1]);
96 two = sm_snprintf(dst2, sizeof dst2, "%s/%s", src1[0], src1[1]);
99 one = sm_strlcpyn(dst1, 10, 3, src1[0], "/", src1[1]);
100 two = sm_snprintf(dst2, 10, "%s/%s", src1[0], src1[1]);
103 one = sm_strlcpyn(dst1, 5, 3, src1[0], "/", src1[1]);
104 two = sm_snprintf(dst2, 5, "%s/%s", src1[0], src1[1]);
107 one = sm_strlcpyn(dst1, 0, 3, src1[0], "/", src1[1]);
108 two = sm_snprintf(dst2, 0, "%s/%s", src1[0], src1[1]);
[all …]
/freebsd/contrib/llvm-project/clang/lib/Headers/
H A Damxfp8intrin.h23 _tile1024i dst, _tile1024i src1, _tile1024i src2) { in _tile_dpbf8ps_internal() argument
24 return __builtin_ia32_tdpbf8ps_internal(m, n, k, dst, src1, src2); in _tile_dpbf8ps_internal()
65 __tile_dpbf8ps(__tile1024i *dst, __tile1024i src1, __tile1024i src2) { in __tile_dpbf8ps() argument
66 dst->tile = _tile_dpbf8ps_internal(src1.row, src2.col, src1.col, dst->tile, in __tile_dpbf8ps()
67 src1.tile, src2.tile); in __tile_dpbf8ps()
72 _tile1024i dst, _tile1024i src1, _tile1024i src2) { in _tile_dpbhf8ps_internal() argument
73 return __builtin_ia32_tdpbhf8ps_internal(m, n, k, dst, src1, src2); in _tile_dpbhf8ps_internal()
114 __tile_dpbhf8ps(__tile1024i *dst, __tile1024i src1, __tile1024i src2) { in __tile_dpbhf8ps() argument
115 dst->tile = _tile_dpbhf8ps_internal(src1.row, src2.col, src1.col, dst->tile, in __tile_dpbhf8ps()
116 src1.tile, src2.tile); in __tile_dpbhf8ps()
[all …]
H A Damxintrin.h151 #define _tile_dpbssd(dst, src0, src1) \ argument
152 __builtin_ia32_tdpbssd((dst), (src0), (src1))
170 #define _tile_dpbsud(dst, src0, src1) \ argument
171 __builtin_ia32_tdpbsud((dst), (src0), (src1))
189 #define _tile_dpbusd(dst, src0, src1) \ argument
190 __builtin_ia32_tdpbusd((dst), (src0), (src1))
208 #define _tile_dpbuud(dst, src0, src1) \ argument
209 __builtin_ia32_tdpbuud((dst), (src0), (src1))
226 #define _tile_dpbf16ps(dst, src0, src1) \ argument
227 __builtin_ia32_tdpbf16ps((dst), (src0), (src1))
[all …]
H A Damxcomplextransposeintrin.h193 _tile1024i src1, _tile1024i src2) { in _tile_tcmmimfp16ps_internal() argument
194 return __builtin_ia32_ttcmmimfp16ps_internal(m, n, k, dst, src1, src2); in _tile_tcmmimfp16ps_internal()
199 _tile1024i src1, _tile1024i src2) { in _tile_tcmmrlfp16ps_internal() argument
200 return __builtin_ia32_ttcmmrlfp16ps_internal(m, n, k, dst, src1, src2); in _tile_tcmmrlfp16ps_internal()
205 _tile1024i src1, _tile1024i src2) { in _tile_conjtcmmimfp16ps_internal() argument
206 return __builtin_ia32_tconjtcmmimfp16ps_internal(m, n, k, dst, src1, src2); in _tile_conjtcmmimfp16ps_internal()
232 __tile1024i src1) { in __tile_tcmmimfp16ps() argument
233 dst->tile = _tile_tcmmimfp16ps_internal(src0.row, src1.col, src0.col, in __tile_tcmmimfp16ps()
234 dst->tile, src0.tile, src1.tile); in __tile_tcmmimfp16ps()
255 __tile1024i src1) { in __tile_tcmmrlfp16ps() argument
[all …]
H A Damxcomplexintrin.h112 _tile1024i dst, _tile1024i src1, _tile1024i src2) { in _tile_cmmimfp16ps_internal() argument
113 return __builtin_ia32_tcmmimfp16ps_internal(m, n, k, dst, src1, src2); in _tile_cmmimfp16ps_internal()
118 _tile1024i dst, _tile1024i src1, _tile1024i src2) { in _tile_cmmrlfp16ps_internal() argument
119 return __builtin_ia32_tcmmrlfp16ps_internal(m, n, k, dst, src1, src2); in _tile_cmmrlfp16ps_internal()
139 __tile_cmmimfp16ps(__tile1024i *dst, __tile1024i src0, __tile1024i src1) { in __tile_cmmimfp16ps() argument
140 dst->tile = _tile_cmmimfp16ps_internal(src0.row, src1.col, src0.col, in __tile_cmmimfp16ps()
141 dst->tile, src0.tile, src1.tile); in __tile_cmmimfp16ps()
161 __tile_cmmrlfp16ps(__tile1024i *dst, __tile1024i src0, __tile1024i src1) { in __tile_cmmrlfp16ps() argument
162 dst->tile = _tile_cmmrlfp16ps_internal(src0.row, src1.col, src0.col, in __tile_cmmrlfp16ps()
163 dst->tile, src0.tile, src1.tile); in __tile_cmmrlfp16ps()
H A Damxavx512intrin.h283 static __m512 __tile_cvtrowd2ps(__tile1024i src0, unsigned src1) { in __tile_cvtrowd2ps() argument
284 return _tile_cvtrowd2ps_internal(src0.row, src0.col, src0.tile, src1); in __tile_cvtrowd2ps()
302 static __m512bh __tile_cvtrowps2bf16h(__tile1024i src0, unsigned src1) { in __tile_cvtrowps2bf16h() argument
303 return _tile_cvtrowps2bf16h_internal(src0.row, src0.col, src0.tile, src1); in __tile_cvtrowps2bf16h()
321 static __m512bh __tile_cvtrowps2bf16l(__tile1024i src0, unsigned src1) { in __tile_cvtrowps2bf16l() argument
322 return _tile_cvtrowps2bf16l_internal(src0.row, src0.col, src0.tile, src1); in __tile_cvtrowps2bf16l()
340 static __m512h __tile_cvtrowps2phh(__tile1024i src0, unsigned src1) { in __tile_cvtrowps2phh() argument
341 return _tile_cvtrowps2phh_internal(src0.row, src0.col, src0.tile, src1); in __tile_cvtrowps2phh()
359 static __m512h __tile_cvtrowps2phl(__tile1024i src0, unsigned src1) { in __tile_cvtrowps2phl() argument
360 return _tile_cvtrowps2phl_internal(src0.row, src0.col, src0.tile, src1); in __tile_cvtrowps2phl()
[all …]
/freebsd/contrib/llvm-project/llvm/lib/Target/X86/
H A DX86InstrAMX.td65 def PTILELOADDV : PseudoI<(outs TILE:$dst), (ins GR16:$src1,
69 def PTILELOADDT1V : PseudoI<(outs TILE:$dst), (ins GR16:$src1,
73 def PTILESTOREDV : PseudoI<(outs), (ins GR16:$src1,
78 def PTILEZEROV : PseudoI<(outs TILE:$dst), (ins GR16:$src1, GR16:$src2),
80 GR16:$src1, GR16:$src2))]>;
86 def PTILELOADD : PseudoI<(outs), (ins u8imm:$src1, sibmem:$src2), []>;
88 def PTILELOADDT1 : PseudoI<(outs), (ins u8imm:$src1,
100 let Constraints = "$src1 = $dst" in {
102 (ins TILE:$src1, TILE:$src2, TILE:$src3),
106 (ins TILE:$src1, TILE:$src2, TILE:$src3),
[all …]
H A DX86InstrXOP.td97 (ins VR128:$src1, VR128:$src2),
98 !strconcat(OpcodeStr, "\t{$src2, $src1, $dst|$dst, $src1, $src2}"),
100 (vt128 (OpNode (vt128 VR128:$src1), (vt128 VR128:$src2))))]>,
103 (ins VR128:$src1, i128mem:$src2),
104 !strconcat(OpcodeStr, "\t{$src2, $src1, $dst|$dst, $src1, $src2}"),
106 (vt128 (OpNode (vt128 VR128:$src1),
110 (ins i128mem:$src1, VR128:$src2),
111 !strconcat(OpcodeStr, "\t{$src2, $src1,
[all...]
H A DX86InstrShiftRotate.td244 def : Pat<(rotl GR8:$src1, (i8 7)), (ROR8r1 GR8:$src1)>;
245 def : Pat<(rotl GR16:$src1, (i8 15)), (ROR16r1 GR16:$src1)>;
246 def : Pat<(rotl GR32:$src1, (i8 31)), (ROR32r1 GR32:$src1)>;
247 def : Pat<(rotl GR64:$src1, (i8 63)), (ROR64r1 GR64:$src1)>;
248 def : Pat<(rotr GR8:$src1, (i8 7)), (ROL8r1 GR8:$src1)>;
[all...]
H A DX86InstrCMovSetCC.td19 (ins t.RegClass:$src1, t.RegClass:$src2, ccode:$cond),
21 [(set t.RegClass:$dst, (X86cmov t.RegClass:$src1,
25 (ins t.RegClass:$src1, t.MemOperand:$src2, ccode:$cond),
27 [(set t.RegClass:$dst, (X86cmov t.RegClass:$src1,
35 (ins t.RegClass:$src1, ccode:$cond),
38 (X86cmov 0, t.RegClass:$src1, timm:$cond, EFLAGS))]>, UseEFLAGS, NF;
40 (ins t.RegClass:$src1, ccode:$cond),
46 (ins t.RegClass:$src1, t.RegClass:$src2, ccode:$cond),
52 (ins t.MemOperand:$src1, ccode:$cond),
56 (ins t.RegClass:$src1, t.MemOperand:$src2, ccode:$cond),
[all …]
H A DX86InstrConditionalCompare.td14 : ITy<o, f, t, (outs), (ins op1:$src1, op2:$src2, cflags:$dcf, ccode:$cond),
15 … m#"${cond}", "$dcf\t{$src2, $src1|$src1, $src2}" , []>, T_MAP4, EVEX, Requires<[In64BitMode]> {
81 def : Pat<(X86ccmp GR8:$src1, GR8:$src2, timm:$dcf, timm:$cond, EFLAGS),
82 (CCMP8rr GR8:$src1, GR8:$src2, timm:$dcf, timm:$cond)>;
83 def : Pat<(X86ccmp GR16:$src1, GR16:$src2, timm:$dcf, timm:$cond, EFLAGS),
84 (CCMP16rr GR16:$src1, GR16:$src2, timm:$dcf, timm:$cond)>;
85 def : Pat<(X86ccmp GR32:$src1, GR32:$src2, timm:$dcf, timm:$cond, EFLAGS),
86 (CCMP32rr GR32:$src1, GR32:$src2, timm:$dcf, timm:$cond)>;
87 def : Pat<(X86ccmp GR64:$src1, GR64:$src2, timm:$dcf, timm:$cond, EFLAGS),
88 (CCMP64rr GR64:$src1, GR64:$src2, timm:$dcf, timm:$cond)>;
[all …]
H A DX86InstrKL.td23 (ins VR128:$src1, opaquemem:$src2),
24 "aesenc128kl\t{$src2, $src1|$src1, $src2}",
25 [(set VR128:$dst, EFLAGS, (X86aesenc128kl VR128:$src1, addr:$src2))]>,
28 (ins VR128:$src1, opaquemem:$src2),
29 "aesdec128kl\t{$src2, $src1|$src1, $src2}",
30 [(set VR128:$dst, EFLAGS, (X86aesdec128kl VR128:$src1, addr:$src2))]>,
33 (ins VR128:$src1, opaquemem:$src2),
34 "aesenc256kl\t{$src2, $src1|$src1, $src2}",
35 [(set VR128:$dst, EFLAGS, (X86aesenc256kl VR128:$src1, addr:$src2))]>,
38 (ins VR128:$src1, opaquemem:$src2),
[all …]
H A DX86InstrSSE.td26 def rr : SI<opc, MRMSrcReg, (outs RC:$dst), (ins RC:$src1, RC:$src2),
29 !strconcat(OpcodeStr, "\t{$src2, $src1, $dst|$dst, $src1, $src2}")),
30 [(set RC:$dst, (OpNode RC:$src1, RC:$src2))], d>,
33 def rm : SI<opc, MRMSrcMem, (outs RC:$dst), (ins RC:$src1, x86memop:$src2),
36 !strconcat(OpcodeStr, "\t{$src2, $src1, $dst|$dst, $src1, $src2}")),
37 [(set RC:$dst, (OpNode RC:$src1, (load addr:$src2)))], d>,
49 def rr_Int : SI_Int<opc, MRMSrcReg, (outs RC:$dst), (ins RC:$src1, RC:$src2),
52 !strconcat(asm, "\t{$src2, $src1, $dst|$dst, $src1, $src2}")),
53 [(set RC:$dst, (VT (OpNode RC:$src1, RC:$src2)))], d>,
56 def rm_Int : SI_Int<opc, MRMSrcMem, (outs RC:$dst), (ins RC:$src1, memopr:$src2),
[all …]
H A DX86InstrFMA.td40 (ins RC:$src1, RC:$src2, RC:$src3),
43 [(set RC:$dst, (VT (Op RC:$src2, RC:$src1, RC:$src3)))]>,
48 (ins RC:$src1, RC:$src2, x86memop:$src3),
51 [(set RC:$dst, (VT (Op RC:$src2, RC:$src1,
61 (ins RC:$src1, RC:$src2, RC:$src3),
68 (ins RC:$src1, RC:$src2, x86memop:$src3),
72 RC:$src1)))]>,
81 (ins RC:$src1, RC:$src2, RC:$src3),
90 (ins RC:$src1, RC:$src2, x86memop:$src3),
93 [(set RC:$dst, (VT (Op (MemFrag addr:$src3), RC:$src1,
[all …]
H A DX86InstrCompiler.td897 def 16m : Ii8<0xBA, Form, (outs), (ins i16mem:$src1, i8imm:$src2),
898 !strconcat(s, "{w}\t{$src2, $src1|$src1, $src2}"),
899 [(set EFLAGS, (!cast<SDNode>("x86" # s) addr:$src1, timm:$src2, (i32 16)))]>,
901 def 32m : Ii8<0xBA, Form, (outs), (ins i32mem:$src1, i8imm:$src2),
902 !strconcat(s, "{l}\t{$src2, $src1|$src1, $src2}"),
903 [(set EFLAGS, (!cast<SDNode>("x86" # s) addr:$src1, timm:$src2, (i32 32)))]>,
905 def 64m : RIi8<0xBA, Form, (outs), (ins i64mem:$src1, i8imm:$src2),
906 !strconcat(s, "{q}\t{$src2, $src1|$src1, $src2}"),
907 [(set EFLAGS, (!cast<SDNode>("x86" # s) addr:$src1, timm:$src2, (i32 64)))]>,
915 def 16rm : I<Opc8, MRMDestMem, (outs), (ins i16mem:$src1, GR16:$src2),
[all …]
H A DX86InstrAsmAlias.td70 def : InstAlias<"ccmp"#Cond#"{b} $dcf\t{$src2, $src1|$src1, $src2}",
71 (CCMP8rr GR8:$src1, GR8:$src2, cflags:$dcf, CC), 0>;
72 def : InstAlias<"ccmp"#Cond#"{w} $dcf\t{$src2, $src1|$src1, $src2}",
73 (CCMP16rr GR16:$src1, GR16:$src2, cflags:$dcf, CC), 0>;
74 def : InstAlias<"ccmp"#Cond#"{l} $dcf\t{$src2, $src1|$src1, $src2}",
75 (CCMP32rr GR32:$src1, GR32:$src2, cflags:$dcf, CC), 0>;
76 def : InstAlias<"ccmp"#Cond#"{q} $dcf\t{$src2, $src1|$src1, $src2}",
77 (CCMP64rr GR64:$src1, GR64:$src2, cflags:$dcf, CC), 0>;
78 def : InstAlias<"ccmp"#Cond#"{b} $dcf\t{$src2, $src1|$src1, $src2}",
79 (CCMP8rm GR8:$src1, i8mem:$src2, cflags:$dcf, CC), 0>;
[all …]
H A DX86InstrVMX.td19 def INVEPT32 : I<0x80, MRMSrcMem, (outs), (ins GR32:$src1, i128mem:$src2),
20 "invept\t{$src2, $src1|$src1, $src2}", []>, T8, PD,
22 def INVEPT64 : I<0x80, MRMSrcMem, (outs), (ins GR64:$src1, i128mem:$src2),
23 "invept\t{$src2, $src1|$src1, $src2}", []>, T8, PD,
25 def INVEPT64_EVEX : I<0xF0, MRMSrcMem, (outs), (ins GR64:$src1, i128mem:$src2),
26 "invept\t{$src2, $src1|$src1, $src2}", []>,
30 def INVVPID32 : I<0x81, MRMSrcMem, (outs), (ins GR32:$src1, i128mem:$src2),
31 "invvpid\t{$src2, $src1|$src1, $src2}", []>, T8, PD,
33 def INVVPID64 : I<0x81, MRMSrcMem, (outs), (ins GR64:$src1, i128mem:$src2),
34 "invvpid\t{$src2, $src1|$src1, $src2}", []>, T8, PD,
[all …]
/freebsd/contrib/llvm-project/llvm/lib/Target/AMDGPU/
H A DAMDGPUInstrInfo.td214 // out = (src0 + src1 > 0xFFFFFFFF) ? 1 : 0
217 // out = (src1 > src0) ? 1 : 0
254 // src1 = Denominator, src2 = Numerator).
259 // Special case divide fixup and flags(src0 = Quotient, src1 =
279 // src1: dst - rat offset (aka pointer) in dwords
356 SDTCisSameAs<3, 2>, // f32 src1
428 def AMDGPUfp_class : PatFrags<(ops node:$src0, node:$src1),
429 [(int_amdgcn_class node:$src0, node:$src1),
430 (AMDGPUfp_class_impl node:$src0, node:$src1)]>;
432 def AMDGPUfmed3 : PatFrags<(ops node:$src0, node:$src1, node:$src2),
[all …]
/freebsd/contrib/arm-optimized-routines/string/aarch64/
H A Dmemcmp.S14 #define src1 x0 macro
35 ldp data1, data3, [src1]
41 add src1end, src1, limit
51 ldp data1, data3, [src1, 16]
59 ldp data1, data3, [src1, 32]
64 add src1, src1, 32
92 add src1end, src1, limit
95 ldr data1, [src1]
104 ldr data1w, [src1]
112 ldrh data1w, [src1]
[all …]
H A Dstrcmp.S20 #define src1 x0 macro
54 sub off2, src2, src1
56 and tmp, src1, 7
64 ldr data2, [src1, off2]
65 ldr data1, [src1], 8
108 bic src1, src1, 7
109 ldr data2, [src1, off2]
110 ldr data1, [src1], 8
123 ldrb data1w, [src1], 1
128 tst src1, 7
[all …]
/freebsd/sys/arm64/arm64/
H A Dstrcmp.S24 #define src1 x0 macro
58 sub off2, src2, src1
60 and tmp, src1, 7
68 ldr data2, [src1, off2]
69 ldr data1, [src1], 8
112 bic src1, src1, 7
113 ldr data2, [src1, off2]
114 ldr data1, [src1], 8
127 ldrb data1w, [src1], 1
132 tst src1, 7
[all …]
H A Dmemcmp.S19 #define src1 x0 macro
38 ldr data1, [src1], 8
46 ldr data1, [src1, limit]
51 ldr data1, [src1], 8
67 and tmp1, src1, 15
69 sub src1, src1, tmp1
77 ldp data1, data1h, [src1], 16
93 add src1, src1, limit
95 ldp data1, data1h, [src1]
120 ldr data1w, [src1], 4
[all …]

12345678