Home
last modified time | relevance | path

Searched refs:VTYPE (Results 1 – 23 of 23) sorted by relevance

/freebsd/contrib/arm-optimized-routines/math/
H A Dpoly_generic.h8 #ifndef VTYPE
9 # error Cannot use poly_generic without defining VTYPE
18 static inline VTYPE VWRAP (pairwise_poly_3) (VTYPE x, VTYPE x2, in VWRAP()
19 const VTYPE *poly) in VWRAP()
22 VTYPE p01 = FMA (poly[1], x, poly[0]); in VWRAP()
23 VTYPE p23 = FMA (poly[3], x, poly[2]); in VWRAP()
27 static inline VTYPE VWRAP (estrin_4) (VTYPE x, VTYPE x2, VTYPE x4, in VWRAP()
28 const VTYPE *poly) in VWRAP()
30 VTYPE p03 = VWRAP (pairwise_poly_3) (x, x2, poly); in VWRAP()
33 static inline VTYPE VWRAP (estrin_5) (VTYPE x, VTYPE x2, VTYPE x4, in VWRAP()
[all …]
H A Dpoly_scalar_f32.h16 #define VTYPE float macro
22 #undef VTYPE
H A Dpoly_scalar_f64.h16 #define VTYPE double macro
22 #undef VTYPE
/freebsd/contrib/arm-optimized-routines/math/aarch64/sve/
H A Dsv_poly_generic.h9 #ifndef VTYPE
10 # error Cannot use poly_generic without defining VTYPE
22 static inline VTYPE VWRAP (pairwise_poly_3) (svbool_t pg, VTYPE x, VTYPE x2, in VWRAP()
26 VTYPE p01 = svmla_x (pg, DUP (poly[0]), x, poly[1]); in VWRAP()
27 VTYPE p23 = svmla_x (pg, DUP (poly[2]), x, poly[3]); in VWRAP()
31 static inline VTYPE VWRAP (estrin_4) (svbool_t pg, VTYPE x, VTYPE x2, VTYPE x4, in VWRAP()
34 VTYPE p03 = VWRAP (pairwise_poly_3) (pg, x, x2, poly); in VWRAP()
37 static inline VTYPE VWRAP (estrin_5) (svbool_t pg, VTYPE x, VTYPE x2, VTYPE x4, in VWRAP()
40 VTYPE p03 = VWRAP (pairwise_poly_3) (pg, x, x2, poly); in VWRAP()
41 VTYPE p45 = svmla_x (pg, DUP (poly[4]), x, poly[5]); in VWRAP()
[all …]
H A Dsv_poly_f64.h16 #define VTYPE svfloat64_t macro
24 #undef VTYPE
H A Dsv_poly_f32.h16 #define VTYPE svfloat32_t macro
24 #undef VTYPE
/freebsd/contrib/llvm-project/llvm/lib/Target/RISCV/
H A DRISCVInstrFormatsV.td71 let Defs = [VL, VTYPE];
87 let Defs = [VL, VTYPE];
104 let Defs = [VL, VTYPE];
123 let Uses = [VL, VTYPE];
143 let Uses = [VL, VTYPE];
162 let Uses = [VL, VTYPE];
182 let Uses = [VL, VTYPE];
201 let Uses = [VL, VTYPE];
223 let Uses = [VL, VTYPE];
245 let Uses = [VL, VTYPE];
[all …]
H A DRISCVInstrInfoXSfmm.td48 let Defs = [VTYPE, VL];
67 let Uses = [VTYPE, VL];
96 let Uses = [VTYPE, VL];
115 let Uses = [VTYPE, VL];
137 let Uses = [VTYPE, VL];
169 let Uses = [VTYPE, VL];
196 let Uses = [VTYPE, VL];
H A DRISCVInstrInfoZvfbf.td24 let Uses = [FRM, VL, VTYPE] in
30 RVVConstraint = WidenV, Uses = [FRM, VL, VTYPE], mayRaiseFPException = true,
H A DRISCVInsertVSETVLI.cpp344 MI.readsRegister(RISCV::VTYPE, /*TRI=*/nullptr)) in getDemanded()
1278 MI.modifiesRegister(RISCV::VTYPE, /*TRI=*/nullptr)) in transferAfter()
1415 MI.getOperand(4).getReg() == RISCV::VTYPE && in emitVSETVLIs()
1428 MI.addOperand(MachineOperand::CreateReg(RISCV::VTYPE, /*isDef*/ false, in emitVSETVLIs()
1479 MI.addOperand(MachineOperand::CreateReg(RISCV::VTYPE, /*isDef*/ false, in emitVSETVLIs()
1486 MI.addOperand(MachineOperand::CreateReg(RISCV::VTYPE, /*isDef*/ true, in emitVSETVLIs()
1492 MI.modifiesRegister(RISCV::VTYPE, /*TRI=*/nullptr)) in emitVSETVLIs()
1679 MI.modifiesRegister(RISCV::VTYPE, /*TRI=*/nullptr)) in coalesceVSETVLIs()
H A DRISCVInstrInfoXRivos.td29 let Uses = [VL, VTYPE];
50 let Uses = [VL, VTYPE];
H A DRISCVInstrInfoV.td1378 let Uses = [FRM, VL, VTYPE], mayRaiseFPException = true in {
1386 Uses = [FRM, VL, VTYPE],
1401 } // Constraints = "@earlyclobber $vd", Uses = [FRM, VL, VTYPE], mayRaiseFPException = true, DestEE…
1404 let Uses = [FRM, VL, VTYPE], mayRaiseFPException = true in {
1412 Uses = [FRM, VL, VTYPE], mayRaiseFPException = true, DestEEW = EEWSEWx2 in {
1414 } // Constraints = "@earlyclobber $vd", RVVConstraint = WidenV, Uses = [FRM, VL, VTYPE], mayRaiseFP…
1417 let Uses = [FRM, VL, VTYPE], mayRaiseFPException = true in {
1429 let Uses = [FRM, VL, VTYPE], mayRaiseFPException = true, DestEEW = EEWSEWx2 in {
1434 } // Constraints = "@earlyclobber $vd", RVVConstraint = WidenV, Uses = [FRM, VL, VTYPE], mayRaiseFP…
1437 let Uses = [FRM, VL, VTYPE], mayRaiseFPException = true in {
[all …]
H A DRISCVInstrInfoXAndes.td424 let Uses = [VL, VTYPE];
446 let Uses = [VTYPE, VL];
665 let Uses = [FRM, VL, VTYPE] in
683 Uses = [FRM, VL, VTYPE], mayRaiseFPException = true in {
692 let Predicates = [HasVendorXAndesVDot], Uses = [VL, VTYPE] in {
H A DRISCVInstrPredicates.td80 // VL and only sets VTYPE.
H A DRISCVInstrInfoXSf.td74 let Uses = [VL, VTYPE];
98 let Uses = [VL, VTYPE];
240 Uses = [FRM, VL, VTYPE] in {
H A DRISCVRegisterInfo.td709 def VTYPE : RISCVReg<0, "vtype">;
718 (add VTYPE, VL, VLENB)> {
H A DRISCVRegisterInfo.cpp160 markSuperRegs(Reserved, RISCV::VTYPE); in getReservedRegs()
H A DRISCVFrameLowering.cpp2268 (MBB.isLiveIn(RISCV::VTYPE) || MBB.isLiveIn(RISCV::VL))) in canUseAsPrologue()
H A DRISCVInstrInfoZvk.td49 let Uses = [VL, VTYPE];
H A DRISCVInstrInfoVPseudos.td15 /// have behavior which depends on the value of VTYPE. Several core aspects of
46 /// about the value of VTYPE.
6077 let Defs = [VL, VTYPE] in {
6110 let hasSideEffects = 0, mayLoad = 0, mayStore = 0, Defs = [VL, VTYPE] in {
H A DRISCVInstrInfo.cpp495 MIB.addReg(RISCV::VTYPE, RegState::Implicit); in copyPhysRegVector()
/freebsd/contrib/arm-optimized-routines/math/aarch64/advsimd/
H A Dv_poly_f64.h16 #define VTYPE float64x2_t macro
22 #undef VTYPE
H A Dv_poly_f32.h16 #define VTYPE float32x4_t macro
22 #undef VTYPE