Home
last modified time | relevance | path

Searched refs:YMM (Results 1 – 18 of 18) sorted by relevance

/freebsd/contrib/llvm-project/lldb/source/Plugins/ABI/X86/
H A DABIX86.cpp178 #define YMM(n) \ macro
196 YMM(0), YMM(1), YMM(2), YMM(3), YMM(4), YMM(5), YMM(6), YMM(7)}}; in makeBaseRegMap()
204 YMM(8), YMM(9), YMM(10), YMM(11), YMM(12), in makeBaseRegMap()
205 YMM(13), YMM(14), YMM(15)}}; in makeBaseRegMap()
/freebsd/contrib/llvm-project/llvm/lib/Target/X86/
H A DX86Schedule.td85 X86FoldableSchedWrite YMM = s256; // YMM operations.
121 X86SchedWriteMoveLS YMM = s256; // YMM operations.
246 defm WriteFAddY : X86SchedWritePair<ReadAfterVecYLd>; // Floating point add/sub (YMM).
250 defm WriteFAdd64Y : X86SchedWritePair<ReadAfterVecYLd>; // Floating point double add/sub (YMM).
254 defm WriteFCmpY : X86SchedWritePair<ReadAfterVecYLd>; // Floating point compare (YMM).
258 defm WriteFCmp64Y : X86SchedWritePair<ReadAfterVecYLd>; // Floating point double compare (YMM).
264 defm WriteFMulY : X86SchedWritePair<ReadAfterVecYLd>; // Floating point multiplication (YMM).
265 defm WriteFMulZ : X86SchedWritePair<ReadAfterVecYLd>; // Floating point multiplication (YMM)
[all...]
H A DX86ScheduleZnver3.td888 defm : Zn3WriteResYMMPair<WriteFAddY, [Zn3FPFAdd01], 3, [1], 1>; // Floating point add/sub (YMM).
892 …Zn3WriteResYMMPair<WriteFAdd64Y, [Zn3FPFAdd01], 3, [1], 1>; // Floating point double add/sub (YMM).
896 defm : Zn3WriteResYMMPair<WriteFCmpY, [Zn3FPFMul01], 1, [1], 1>; // Floating point compare (YMM).
900 …Zn3WriteResYMMPair<WriteFCmp64Y, [Zn3FPFMul01], 1, [1], 1>; // Floating point double compare (YMM).
906 …: Zn3WriteResYMMPair<WriteFMulY, [Zn3FPFMul01], 3, [1], 1>; // Floating point multiplication (YMM).
907 defm : X86WriteResPairUnsupported<WriteFMulZ>; // Floating point multiplication (YMM).
910 …eResYMMPair<WriteFMul64Y, [Zn3FPFMul01], 3, [1], 1>; // Floating point double multiplication (YMM).
914 defm : Zn3WriteResYMMPair<WriteFDivY, [Zn3FPFDiv], 11, [3], 1>; // Floating point division (YMM).
918 …Zn3WriteResYMMPair<WriteFDiv64Y, [Zn3FPFDiv], 13, [5], 1>; // Floating point double division (YMM).
922 …m : Zn3WriteResYMMPair<WriteFSqrtY, [Zn3FPFDiv], 15, [5], 1>; // Floating point square root (YMM).
[all …]
H A DX86ScheduleZnver4.td899 defm : Zn4WriteResYMMPair<WriteFAddY, [Zn4FPFAdd01], 3, [1], 1>; // Floating point add/sub (YMM).
903 …Zn4WriteResYMMPair<WriteFAdd64Y, [Zn4FPFAdd01], 3, [1], 1>; // Floating point double add/sub (YMM).
907 defm : Zn4WriteResYMMPair<WriteFCmpY, [Zn4FPFMul01], 2, [1], 1>; // Floating point compare (YMM).
911 …Zn4WriteResYMMPair<WriteFCmp64Y, [Zn4FPFMul01], 2, [1], 1>; // Floating point double compare (YMM).
917 …: Zn4WriteResYMMPair<WriteFMulY, [Zn4FPFMul01], 3, [1], 1>; // Floating point multiplication (YMM).
921 …eResYMMPair<WriteFMul64Y, [Zn4FPFMul01], 3, [1], 1>; // Floating point double multiplication (YMM).
925 defm : Zn4WriteResYMMPair<WriteFDivY, [Zn4FPFDiv], 11, [3], 1>; // Floating point division (YMM).
929 …Zn4WriteResYMMPair<WriteFDiv64Y, [Zn4FPFDiv], 13, [5], 1>; // Floating point double division (YMM).
933 …m : Zn4WriteResYMMPair<WriteFSqrtY, [Zn4FPFDiv], 15, [5], 1>; // Floating point square root (YMM).
937 …riteResYMMPair<WriteFSqrt64Y, [Zn4FPFDiv], 21, [9], 1>; // Floating point double square root (YMM).
[all …]
H A DX86SchedBroadwell.td263 defm : BWWriteResPair<WriteFAddY, [BWPort1], 3, [1], 1, 6>; // Floating point add/sub (YMM/ZMM).
267 …BWWriteResPair<WriteFAdd64Y, [BWPort1], 3, [1], 1, 6>; // Floating point double add/sub (YMM/ZMM).
272 defm : BWWriteResPair<WriteFCmpY, [BWPort1], 3, [1], 1, 6>; // Floating point compare (YMM/ZMM).
276 …BWWriteResPair<WriteFCmp64Y, [BWPort1], 3, [1], 1, 6>; // Floating point double compare (YMM/ZMM).
284 …BWWriteResPair<WriteFMulY, [BWPort01], 3, [1], 1, 6>; // Floating point multiplication (YMM/ZMM).
288 …ResPair<WriteFMul64Y, [BWPort01], 3, [1], 1, 6>; // Floating point double multiplication (YMM/ZMM).
293 …teFDivY, [BWPort0,BWPort015,BWFPDivider], 17, [2,1,10], 3, 6>; // Floating point division (YMM).
297 …teFDiv64Y, [BWPort0,BWPort015,BWFPDivider], 23, [2,1,16], 3, 6>; // Floating point division (YMM).
302 …riteFRcpY, [BWPort0,BWPort015], 11, [2,1], 3, 6>; // Floating point reciprocal estimate (YMM/ZMM).
307 …[BWPort0,BWPort015], 11, [2,1], 3, 6>; // Floating point reciprocal square root estimate (YMM/ZMM).
[all …]
H A DX86CallingConv.td47 list<Register> YMM = [];
59 let YMM = [YMM0, YMM1, YMM2, YMM3, YMM4, YMM5, YMM6, YMM7];
73 let YMM = [YMM0, YMM1, YMM2, YMM3, YMM4, YMM5, YMM6, YMM7];
80 let YMM = [YMM0, YMM1, YMM2, YMM3, YMM4, YMM5, YMM6, YMM7,
151 // __m256, __m256i, __m256d --> YMM
154 CCIfSubtarget<"hasAVX()", CCAssignToReg<RC.YMM>>>,
228 // __m256, __m256i, __m256d --> YMM
230 CCIfSubtarget<"hasAVX()", CCAssignToReg<RC.YMM>>>,
596 // The first 8 256-bit vector arguments are passed in YMM registers, unless
799 // AVX 256-bit vector arguments are passed in YMM registers.
[all …]
H A DX86InstrFMA.td113 VR256, OpTy256, f256mem, MemFrag256, Op, sched.YMM>,
116 VR256, OpTy256, f256mem, MemFrag256, Op, sched.YMM>,
119 VR256, OpTy256, f256mem, MemFrag256, Op, sched.YMM>,
504 REX_W, VEX_L, Sched<[sched.YMM]>;
511 Sched<[sched.YMM.Folded, sched.YMM.ReadAfterFold, sched.YMM.ReadAfterFold]>;
518 Sched<[sched.YMM.Folded, sched.YMM.ReadAfterFold,
523 sched.YMM.ReadAfterFold]>;
535 VEX_L, Sched<[sched.YMM]>;
H A DX86InstrSSE.td367 SSEPackedSingle, SchedWriteFMoveLS.YMM>,
370 SSEPackedDouble, SchedWriteFMoveLS.YMM>,
373 SSEPackedSingle, SchedWriteFMoveLS.YMM>,
376 SSEPackedDouble, SchedWriteFMoveLS.YMM>,
417 let SchedRW = [SchedWriteFMoveLS.YMM.MR] in {
459 let SchedRW = [SchedWriteFMoveLS.YMM.RR] in {
1575 // YMM only
1673 // YMM only
2001 SchedWriteFCmpSizes.PS.YMM, SSEPackedSingle, loadv8f32>, TB, VEX, VVVV, VEX_L, WIG;
2004 … SchedWriteFCmpSizes.PD.YMM, SSEPackedDouble, loadv4f64>, TB, PD, VEX, VVVV, VEX_L, WIG;
[all …]
H A DX86InstrXOP.td82 SchedWriteFRnd.YMM>;
91 SchedWriteFRnd.YMM>;
371 SchedWriteShuffle.YMM>, VEX_L;
462 SchedWriteFVarShuffle.YMM>, VEX_L;
471 SchedWriteFVarShuffle.YMM>, VEX_L;
H A DX86InstrAVX512.td1291 Sched<[SchedWriteShuffle.YMM.Folded]>,
1307 Sched<[SchedWriteShuffle.YMM.Folded]>,
1895 defm Z256 : WriteFVarBlendask<opc, OpcodeStr, sched.YMM, VTInfo.info256>,
1896 WriteFVarBlendask_rmb<opc, OpcodeStr, sched.YMM, VTInfo.info256>,
1911 defm Z256 : WriteFVarBlendask<opc, OpcodeStr, sched.YMM, VTInfo.info256>,
2067 defm Z256 : avx512_icmp_packed<opc, OpcodeStr, sched.YMM,
2083 defm Z256 : avx512_icmp_packed_rmb<opc, OpcodeStr, sched.YMM,
2239 sched.YMM, VTInfo.info256, NAME>, EVEX_V256;
2254 sched.YMM, VTInfo.info256, NAME>, EVEX_V256;
2426 defm Z256 : avx512_vcmp_common<sched.YMM, _.info256, NAME>, EVEX_V256;
[all …]
H A DX86RegisterInfo.td385 def YMM#Index : X86Reg<"ymm"#Index, Index, [!cast<X86Reg>("XMM"#Index)]>,
391 def YMM#Index : X86Reg<"ymm"#Index, Index, [!cast<X86Reg>("XMM"#Index)]>,
400 def ZMM#Index : X86Reg<"zmm"#Index, Index, [!cast<X86Reg>("YMM"#Index)]>,
774 256, (sequence "YMM%u", 0, 15)>;
809 256, (sequence "YMM%u", 0, 31)>;
H A DX86ScheduleZnver1.td985 //=== Floating Point XMM and YMM Instructions ===//
1359 // AVX YMM Zero-idioms.
1391 // AVX YMM
H A DX86ScheduleZnver2.td993 //=== Floating Point XMM and YMM Instructions ===//
1365 // AVX YMM Zero-idioms.
1397 // AVX YMM
H A DX86SchedHaswell.td860 //=== Floating Point XMM and YMM Instructions ===//
/freebsd/contrib/llvm-project/lldb/source/Plugins/Process/Utility/
H A DRegisterContext_x86.h306 struct YMM { struct
329 YMM = SSE << 1, enumerator
330 BNDREGS = YMM << 1,
H A DRegisterContextPOSIX_x86.h157 lldb_private::YMM m_ymm_set; // copy of ymmh and xmm register halves.
H A DRegisterContextPOSIX_x86.cpp403 ::memset(&m_ymm_set, 0, sizeof(YMM)); in RegisterContextPOSIX_x86()
/freebsd/crypto/openssl/doc/man3/
H A DOPENSSL_ia32cap.pod56 =item bit #59, OSXSAVE bit, denoting availability of YMM registers;