Home
last modified time | relevance | path

Searched refs:f16 (Results 1 – 25 of 156) sorted by relevance

1234567

/freebsd/contrib/llvm-project/llvm/lib/Target/RISCV/
H A DRISCVInstrInfoZfh.td275 def : Pat<(f16 (fcopysign FPR16:$rs1, (f16 (fneg FPR16:$rs2)))), (FSGNJN_H $rs1, $rs2)>;
375 def : Pat<(XLenVT (strict_fsetccs (f16 FPR16:$rs1), (f16 FPR16:$rs1), SETEQ)),
377 def : Pat<(XLenVT (strict_fsetccs (f16 FPR16:$rs1), (f16 FPR16:$rs1), SETOEQ)),
417 def : LdPat<load, FLH, f16>;
420 def : StPat<store, FSH, FPR16, f16>;
429 def : Pat<(store (f16 FPR16INX:$rs2),
437 // f32 -> f16, f16 -> f32
452 // f32 -> f16, f16 -> f32
566 // f64 -> f16, f16 -> f64
578 // f64 -> f16, f16 -> f64
[all …]
H A DRISCVInstrInfoZfa.td242 def: PatFprFpr<fminimum, FMINM_H, FPR16, f16>;
243 def: PatFprFpr<fmaximum, FMAXM_H, FPR16, f16>;
247 def: Pat<(f16 (any_frint FPR16:$rs1)), (FROUNDNX_H FPR16:$rs1, FRM_DYN)>;
252 def: Pat<(f16 (any_fround FPR16:$rs1)), (FROUND_H FPR16:$rs1, FRM_RMM)>;
254 def: Pat<(f16 (any_ffloor FPR16:$rs1)), (FROUND_H FPR16:$rs1, FRM_RDN)>;
255 def: Pat<(f16 (any_fceil FPR16:$rs1)), (FROUND_H FPR16:$rs1, FRM_RUP)>;
256 def: Pat<(f16 (any_ftrunc FPR16:$rs1)), (FROUND_H FPR16:$rs1, FRM_RTZ)>;
258 def: PatSetCC<FPR16, strict_fsetcc, SETLT, FLTQ_H, f16>;
259 def: PatSetCC<FPR16, strict_fsetcc, SETOLT, FLTQ_H, f16>;
260 def: PatSetCC<FPR16, strict_fsetcc, SETLE, FLEQ_H, f16>;
[all …]
/freebsd/contrib/llvm-project/llvm/lib/Target/ARM/
H A DARMInstrVFP.td2252 (VFMAH (f16 HPR:$Sdin), (f16 HPR:$Sn), (f16 HPR:$Sm))>,
2303 def : Pat<(f16 (fma (fneg (f16 HPR:$Sn)), (f16 HPR:$Sm), (f16 HPR:$Sdin))),
2304 (VFMSH (f16 HPR:$Sdin), (f16 HPR:$Sn), (f16 HPR:$Sm))>,
2352 def : Pat<(fneg (fma (f16 HPR:$Sn), (f16 HPR:$Sm), (f16 (f16 HPR:$Sdin)))),
2353 (VFNMAH (f16 HPR:$Sdin), (f16 HPR:$Sn), (f16 HPR:$Sm))>,
2362 def : Pat<(f16 (fma (fneg (f16 HPR:$Sn)), (f16 HPR:$Sm), (fneg (f16 HPR:$Sdin)))),
2363 (VFNMAH (f16 HPR:$Sdin), (f16 HPR:$Sn), (f16 HPR:$Sm))>,
2410 def : Pat<(f16 (fma (f16 HPR:$Sn), (f16 HPR:$Sm), (fneg (f16 HPR:$Sdin)))),
2411 (VFNMSH (f16 HPR:$Sdin), (f16 HPR:$Sn), (f16 HPR:$Sm))>,
2420 def : Pat<(fneg (f16 (fma (fneg (f16 HPR:$Sn)), (f16 HPR:$Sm), (f16 HPR:$Sdin)))),
[all …]
/freebsd/crypto/openssl/crypto/aes/asm/
H A Daest4-sparcv9.pl136 ldd [$key + 32], %f16
149 ldd [$key + 16], %f16
214 ldd [$key + 32], %f16
227 ldd [$key + 16], %f16
610 ldd [$key + 208], %f16
628 ldd [$key + 16], %f16
644 ldd [$key + 208], %f16
670 ldd [$key + 16], %f16
720 ldd [$key + 208], %f16
738 ldd [$key + 16], %f16
[all …]
/freebsd/contrib/llvm-project/llvm/include/llvm/CodeGen/
H A DValueTypes.td157 def v1f16 : VTVec<1, f16, 86>; // 1 x f16 vector value
158 def v2f16 : VTVec<2, f16, 87>; // 2 x f16 vector value
159 def v3f16 : VTVec<3, f16, 88>; // 3 x f16 vector value
160 def v4f16 : VTVec<4, f16, 89>; // 4 x f16 vector value
161 def v8f16 : VTVec<8, f16, 90>; // 8 x f16 vector value
162 def v16f16 : VTVec<16, f16, 91>; // 16 x f16 vector value
163 def v32f16 : VTVec<32, f16, 92>; // 32 x f16 vector value
164 def v64f16 : VTVec<64, f16, 93>; // 64 x f16 vector value
165 def v128f16 : VTVec<128, f16, 94>; // 128 x f16 vector value
166 def v256f16 : VTVec<256, f16, 95>; // 256 x f16 vector value
[all …]
/freebsd/crypto/openssl/crypto/camellia/asm/
H A Dcmllt4-sparcv9.pl103 ldd [$key + 32], %f16
121 ldd [$key + 16], %f16
198 ldd [$key - 24], %f16
216 ldd [$key - 24], %f16
349 ldd [%o4 + 0], %f16
618 ldd [$key + 208], %f16
648 ldd [$key + 16], %f16
672 ldd [$key + 208], %f16
718 ldd [$key + 16], %f16
746 ldd [$key - 8], %f16
[all …]
/freebsd/crypto/openssl/crypto/des/asm/
H A Ddest4-sparcv9.pl80 des_kexpand %f14, 1, %f16
82 des_kexpand %f16, 3, %f20
84 des_kexpand %f16, 2, %f18
85 std %f16, [$out + 0x40]
135 ldd [$key + 0x30], %f16
166 des_round %f16, %f18, %f0, %f0
236 ldd [$key + 0x48], %f16
266 des_round %f16, %f18, %f0, %f0
344 ldd [$key + 0x30], %f16
375 des_round %f16, %f18, %f0, %f0
[all …]
/freebsd/contrib/llvm-project/llvm/lib/Target/AMDGPU/
H A DAMDGPUCallingConv.td25 CCIfInReg<CCIfType<[f32, i32, f16, i16, v2i16, v2f16, bf16, v2bf16] , CCAssignToReg<[
32 CCIfNotInReg<CCIfType<[f32, i32, f16, i16, v2i16, v2f16, bf16, v2bf16] , CCAssignToReg<[
39 CCIfType<[i32, f32, v2i16, v2f16, i16, f16, i1, bf16, v2bf16], CCAssignToStack<4, 4>>
46 CCIfNotInReg<CCIfType<[f32, i32, f16, i16, v2i16, v2f16, bf16, v2bf16] , CCAssignToReg<[
69 CCIfInReg<CCIfType<[f32, i32, f16, i16, v2i16, v2f16, bf16, v2bf16] , CCAssignToReg<[
112 CCIfType<[f32, f16, v2f16, bf16, v2bf16] , CCAssignToReg<[
191 CCIfInReg<CCIfType<[f32, i32, f16, i16, v2i16, v2f16, bf16, v2bf16] , CCAssignToReg<
195 CCIfType<[i32, f32, i16, f16, v2i16, v2f16, i1, bf16, v2bf16], CCAssignToReg<[
200 CCIfType<[i32, f32, v2i16, v2f16, i16, f16, i1, bf16, v2bf16], CCAssignToStack<4, 4>>
207 CCIfType<[i32, f32, i16, f16, v2i16, v2f16, bf16, v2bf16], CCAssignToReg<[
[all …]
H A DSIInstructions.td2200 (f16 fpimm:$imm),
2951 (fcanonicalize (f16 (VOP3Mods f16:$src, i32:$src_mods))),
2956 (fcanonicalize (f16 (fneg (VOP3Mods f16:$src, i32:$src_mods)))),
2963 (fcanonicalize (f16 (VOP3Mods f16:$src, i32:$src_mods))),
2968 (fcanonicalize (f16 (fneg (VOP3Mods f16:$src, i32:$src_mods)))),
3027 (fcanonicalize (f16 (VOP3Mods f16:$src, i32:$src_mods))),
3033 (fcanonicalize (f16 (VOP3Mods f16:$src, i32:$src_mods))),
3139 (v2f16 (UniformBinFrag<build_vector> (f16 SReg_32:$src1), (f16 FP_ZERO))),
3159 (v2f16 (build_vector f16:$src0, (f16 undef))),
3175 (v2f16 (UniformBinFrag<build_vector> (f16 undef), (f16 SReg_32:$src1))),
[all …]
H A DVOP3PInstructions.td26 // values are really f16 converted to f32, so we treat these as f16
170 (f16 (fpround (fma_like (f32 (VOP3PMadMixMods f16:$src0, i32:$src0_modifiers)),
184 …(build_vector f16:$elt0, (f16 (fpround (fma_like (f32 (VOP3PMadMixMods f16:$src0, i32:$src0_modifi…
196 f16:$elt0,
197 (AMDGPUclamp (f16 (fpround (fma_like (f32 (VOP3PMadMixMods f16:$src0, i32:$src0_modifiers)),
209 (f16 (fpround (fma_like (f32 (VOP3PMadMixMods f16:$lo_src0, i32:$lo_src0_modifiers)),
212 (f16 (fpround (fma_like (f32 (VOP3PMadMixMods f16:$hi_src0, i32:$hi_src0_modifiers)),
237 …(build_vector f16:$elt0, (f16 (fpround (fmul (f32 (VOP3PMadMixMods f32:$src0, i32:$src0_modifiers)…
257 // Clamp modifier is applied after conversion to f16.
278 // Clamp modifier is applied after conversion to f16.
[all …]
H A DSIInstrInfo.td987 def SDWASrc_f16 : SDWASrc<f16>;
2488 def VOP_F16_F16 : VOPProfile<[f16, f16, untyped, untyped]>;
2493 def VOP_F16_F16_F16 : VOPProfile <[f16, f16, f16, untyped]>;
2494 def VOP_F16_F16_I16 : VOPProfile <[f16, f16, i16, untyped]>;
2495 def VOP_F16_F16_I32 : VOPProfile <[f16, f16, i32, untyped]>;
2500 def VOP_F16_F16_F16_F16 : VOPProfile <[f16, f16, f16, f16, untyped]>;
2508 def VOP_B32_F16_F16 : VOPProfile <[i32, f16, f16, untyped]>;
2515 def VOP_F16_V2F16_V2F16_F16 : VOPProfile <[f16, v2f16, v2f16, f16]>;
2546 def VOP_F32_F16_F16_F16 : VOPProfile <[f32, f16, f16, f16]>;
2552 def VOP_F16_F32_F16_F32 : VOPProfile <[f16, f32, f16, f32]>;
[all …]
H A DSIRegisterInfo.td379 def M0_CLASS_LO16 : SIRegisterClass<"AMDGPU", [i16, f16, bf16], 16, (add M0_LO16)> {
388 def SGPR_LO16 : SIRegisterClass<"AMDGPU", [i16, f16, bf16], 16,
396 def SGPR_HI16 : SIRegisterClass<"AMDGPU", [i16, f16, bf16], 16,
405 def SGPR_32 : SIRegisterClass<"AMDGPU", [i32, f32, i16, f16, bf16, v2i16, v2f16, v2bf16], 32,
461 def TTMP_LO16 : SIRegisterClass<"AMDGPU", [i16, f16, bf16], 16,
587 def Reg16Types : RegisterTypes<[i16, f16, bf16]>;
618 // i16/f16 only on VI+
686 def AGPR_32 : SIRegisterClass<"AMDGPU", [i32, f32, i16, f16, bf16, v2i16, v2f16, v2bf16], 32,
772 def SReg_LO16 : SIRegisterClass<"AMDGPU", [i16, f16, bf16], 16,
803 def SReg_32 : SIRegisterClass<"AMDGPU", [i32, f32, i16, f16, bf16, v2i16, v2f16, v2bf16, i1], 32,
[all …]
H A DVINTERPInstructions.td116 VINTERP_Pseudo <"v_interp_p2_f16_f32", VOP3_VINTERP_F16<[f16, f32, f32, f32]>>;
123 VINTERP_Pseudo <"v_interp_p2_rtz_f16_f32", VOP3_VINTERP_F16<[f16, f32, f32, f32]>>;
174 V_INTERP_P2_F16_F32_inreg, f16,
/freebsd/contrib/llvm-project/llvm/lib/Target/NVPTX/
H A DNVPTXInstrInfo.td1187 def FNEG16 : FNEG_F16_F16X2<"neg.f16", f16, Int16Regs, True>;
1391 defm FMA16 : FMA_F16<"fma.rn.f16", f16, Int16Regs, True>;
2283 // f16 -> pred
2284 def : Pat<(i1 (OpNode (f16 Int16Regs:$a), (f16 Int16Regs:$b))),
2287 def : Pat<(i1 (OpNode (f16 Int16Regs:$a), (f16 Int16Regs:$b))),
2348 // f16 -> i32
2349 def : Pat<(i32 (OpNode (f16 Int16Regs:$a), (f16 Int16Regs:$b))),
3172 // sint -> f16
3182 // uint -> f16
3253 // f16 -> sint
[all …]
/freebsd/crypto/openssl/crypto/sha/asm/
H A Dsha1-sparcv9.pl229 ldd [%o1 + 0x20], %f16
258 ldd [%o1 + 0x18], %f16
270 faligndata %f14, %f16, %f12
271 faligndata %f16, %f18, %f14
272 faligndata %f18, %f20, %f16
H A Dsha512-sparcv9.pl506 ldd [%o1 + 0x00], %f16
570 faligndata %f18, %f20, %f16
612 ldd [%o1 + 0x20], %f16
644 ldd [%o1 + 0x18], %f16
656 faligndata %f14, %f16, %f12
657 faligndata %f16, %f18, %f14
658 faligndata %f18, %f20, %f16
/freebsd/crypto/openssl/crypto/md5/asm/
H A Dmd5-sparcv9.pl247 ldd [%o1 + 0x20], %f16
277 ldd [%o1 + 0x18], %f16
289 faligndata %f14, %f16, %f12
290 faligndata %f16, %f18, %f14
291 faligndata %f18, %f20, %f16
/freebsd/lib/libc/powerpc/gen/
H A D_setjmp.S61 stfd %f16,112+2*8(%r3)
88 lfd %f16,112+2*8(%r3)
H A Dsetjmp.S71 stfd %f16,112+2*8(%r6)
99 lfd %f16,112+2*8(%r3)
H A Dsigsetjmp.S76 stfd %f16,112+2*8(%r6)
103 lfd %f16,112+2*8(%r3)
/freebsd/contrib/llvm-project/llvm/lib/CodeGen/
H A DTargetLoweringBase.cpp246 if (OpVT == MVT::f16) { in getFPEXT()
278 if (RetVT == MVT::f16) { in getFPROUND()
321 if (OpVT == MVT::f16) { in getFPTOSINT()
370 if (OpVT == MVT::f16) { in getFPTOUINT()
420 if (RetVT == MVT::f16) in getSINTTOFP()
433 if (RetVT == MVT::f16) in getSINTTOFP()
446 if (RetVT == MVT::f16) in getSINTTOFP()
466 if (RetVT == MVT::f16) in getUINTTOFP()
479 if (RetVT == MVT::f16) in getUINTTOFP()
492 if (RetVT == MVT::f16) in getUINTTOFP()
[all …]
/freebsd/contrib/arm-optimized-routines/pl/math/
H A Dsv_log1p_2u5.c97 f8 = svmul_x (pg, f4, f4), f16 = svmul_x (pg, f8, f8); in SV_NAME_D1() local
98 svfloat64_t p = sv_estrin_18_f64_x (pg, f, f2, f4, f8, f16, d->poly); in SV_NAME_D1()
/freebsd/usr.sbin/bsdconfig/console/
H A Dfont174 [ "$f8" -a "$f14" -a "$f16" ] || f_die 1 "$msg_unknown_font_selection"
178 f_eval_catch "$0" f_sysrc_set 'f_sysrc_set font8x16 "%s"' "$f16" || f_die
/freebsd/contrib/llvm-project/compiler-rt/lib/xray/
H A Dxray_trampoline_mips64.S39 sdc1 $f16, 32($sp)
66 ldc1 $f16, 32($sp)
/freebsd/contrib/netbsd-tests/ipf/
H A Dt_filter_exec.sh126 test_case f16 mtest text text
159 atf_add_test_case f16

1234567