Home
last modified time | relevance | path

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

/openbsd-src/gnu/llvm/lldb/source/Plugins/ABI/X86/
H A DABIX86.cpp166 #define YMM(n) \ macro
184 YMM(0), YMM(1), YMM(2), YMM(3), YMM(4), YMM(5), YMM(6), YMM(7)}}; in makeBaseRegMap()
192 YMM(8), YMM(9), YMM(10), YMM(11), YMM(12), in makeBaseRegMap()
193 YMM(13), YMM(14), YMM(15)}}; in makeBaseRegMap()
/openbsd-src/gnu/llvm/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).
268 …m WriteFMul64Y : X86SchedWritePair<ReadAfterVecYLd>; // Floating point double multiplication (YMM).
272 defm WriteFDivY : X86SchedWritePair<ReadAfterVecYLd>; // Floating point division (YMM).
[all …]
H A DX86ScheduleZnver3.td891 defm : Zn3WriteResYMMPair<WriteFAddY, [Zn3FPFAdd01], 3, [1], 1>; // Floating point add/sub (YMM).
895 …Zn3WriteResYMMPair<WriteFAdd64Y, [Zn3FPFAdd01], 3, [1], 1>; // Floating point double add/sub (YMM).
899 defm : Zn3WriteResYMMPair<WriteFCmpY, [Zn3FPFMul01], 1, [1], 1>; // Floating point compare (YMM).
903 …Zn3WriteResYMMPair<WriteFCmp64Y, [Zn3FPFMul01], 1, [1], 1>; // Floating point double compare (YMM).
909 …: Zn3WriteResYMMPair<WriteFMulY, [Zn3FPFMul01], 3, [1], 1>; // Floating point multiplication (YMM).
910 defm : X86WriteResPairUnsupported<WriteFMulZ>; // Floating point multiplication (YMM).
913 …eResYMMPair<WriteFMul64Y, [Zn3FPFMul01], 3, [1], 1>; // Floating point double multiplication (YMM).
917 defm : Zn3WriteResYMMPair<WriteFDivY, [Zn3FPFDiv], 11, [3], 1>; // Floating point division (YMM).
921 …Zn3WriteResYMMPair<WriteFDiv64Y, [Zn3FPFDiv], 13, [5], 1>; // Floating point double division (YMM).
925 …m : Zn3WriteResYMMPair<WriteFSqrtY, [Zn3FPFDiv], 15, [5], 1>; // Floating point square root (YMM).
[all …]
H A DX86ScheduleZnver4.td904 defm : Zn4WriteResYMMPair<WriteFAddY, [Zn4FPFAdd01], 3, [1], 1>; // Floating point add/sub (YMM).
908 …Zn4WriteResYMMPair<WriteFAdd64Y, [Zn4FPFAdd01], 3, [1], 1>; // Floating point double add/sub (YMM).
912 defm : Zn4WriteResYMMPair<WriteFCmpY, [Zn4FPFMul01], 2, [2], 1>; // Floating point compare (YMM).
916 …Zn4WriteResYMMPair<WriteFCmp64Y, [Zn4FPFMul01], 2, [2], 1>; // Floating point double compare (YMM).
922 …: Zn4WriteResYMMPair<WriteFMulY, [Zn4FPFMul01], 3, [1], 1>; // Floating point multiplication (YMM).
926 …eResYMMPair<WriteFMul64Y, [Zn4FPFMul01], 3, [1], 1>; // Floating point double multiplication (YMM).
930 defm : Zn4WriteResYMMPair<WriteFDivY, [Zn4FPFDiv], 11, [3], 1>; // Floating point division (YMM).
934 …Zn4WriteResYMMPair<WriteFDiv64Y, [Zn4FPFDiv], 13, [5], 1>; // Floating point double division (YMM).
938 …m : Zn4WriteResYMMPair<WriteFSqrtY, [Zn4FPFDiv], 15, [5], 1>; // Floating point square root (YMM).
942 …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 DX86InstrSSE.td368 SSEPackedSingle, SchedWriteFMoveLS.YMM>,
371 SSEPackedDouble, SchedWriteFMoveLS.YMM>,
374 SSEPackedSingle, SchedWriteFMoveLS.YMM>,
377 SSEPackedDouble, SchedWriteFMoveLS.YMM>,
418 let SchedRW = [SchedWriteFMoveLS.YMM.MR] in {
460 let SchedRW = [SchedWriteFMoveLS.YMM.RR] in {
1582 // YMM only
1666 // YMM only
1994 SchedWriteFCmpSizes.PS.YMM, SSEPackedSingle, loadv8f32>, PS, VEX_4V, VEX_L, VEX_WIG;
1997 SchedWriteFCmpSizes.PD.YMM, SSEPackedDouble, loadv4f64>, PD, VEX_4V, VEX_L, VEX_WIG;
[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 VEX_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]>, FoldGenData<NAME#Yrr>;
H A DX86CallingConv.td42 list<Register> YMM = [];
54 let YMM = [YMM0, YMM1, YMM2, YMM3, YMM4, YMM5, YMM6, YMM7];
61 let YMM = [YMM0, YMM1, YMM2, YMM3, YMM4, YMM5, YMM6, YMM7,
120 // __m256, __m256i, __m256d --> YMM
123 CCIfSubtarget<"hasAVX()", CCAssignToReg<RC.YMM>>>,
197 // __m256, __m256i, __m256d --> YMM
199 CCIfSubtarget<"hasAVX()", CCAssignToReg<RC.YMM>>>,
571 // The first 8 256-bit vector arguments are passed in YMM registers, unless
807 // AVX 256-bit vector arguments are passed in YMM registers.
827 // AVX 256-bit vector arguments are passed in YMM registers.
[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.td1467 Sched<[SchedWriteShuffle.YMM.Folded]>,
1483 Sched<[SchedWriteShuffle.YMM.Folded]>,
2060 defm Z256 : WriteFVarBlendask<opc, OpcodeStr, sched.YMM, VTInfo.info256>,
2061 WriteFVarBlendask_rmb<opc, OpcodeStr, sched.YMM, VTInfo.info256>,
2076 defm Z256 : WriteFVarBlendask<opc, OpcodeStr, sched.YMM, VTInfo.info256>,
2241 defm Z256 : avx512_icmp_packed<opc, OpcodeStr, sched.YMM,
2257 defm Z256 : avx512_icmp_packed_rmb<opc, OpcodeStr, sched.YMM,
2433 sched.YMM, VTInfo.info256, NAME>, EVEX_V256;
2448 sched.YMM, VTInfo.info256, NAME>, EVEX_V256;
2654 defm Z256 : avx512_vcmp_common<sched.YMM, _.info256, NAME>, EVEX_V256;
[all …]
H A DX86RegisterInfo.td247 def YMM#Index : X86Reg<"ymm"#Index, Index, [!cast<X86Reg>("XMM"#Index)]>,
255 def ZMM#Index : X86Reg<"zmm"#Index, Index, [!cast<X86Reg>("YMM"#Index)]>,
572 256, (sequence "YMM%u", 0, 15)>;
607 256, (sequence "YMM%u", 0, 31)>;
H A DX86ScheduleZnver1.td985 //=== Floating Point XMM and YMM Instructions ===//
1367 // AVX YMM Zero-idioms.
1399 // AVX YMM
H A DX86ScheduleZnver2.td993 //=== Floating Point XMM and YMM Instructions ===//
1368 // AVX YMM Zero-idioms.
1400 // AVX YMM
H A DX86SchedHaswell.td859 //=== Floating Point XMM and YMM Instructions ===//
/openbsd-src/gnu/llvm/lldb/source/Plugins/Process/Utility/
H A DRegisterContext_x86.h303 struct YMM { struct
326 YMM = SSE << 1, enumerator
327 BNDREGS = YMM << 1,
H A DRegisterContextPOSIX_x86.h184 lldb_private::YMM m_ymm_set; // copy of ymmh and xmm register halves.
H A DRegisterContextPOSIX_x86.cpp447 ::memset(&m_ymm_set, 0, sizeof(YMM)); in RegisterContextPOSIX_x86()
/openbsd-src/gnu/llvm/lldb/source/Plugins/Process/Linux/
H A DNativeRegisterContextLinux_x86_64.h103 YMM m_ymm_set;
H A DNativeRegisterContextLinux_x86_64.cpp576 xstate_bv |= XSAVE_HDR::XFeature::YMM | XSAVE_HDR::XFeature::SSE; in UpdateXSTATEforWrite()
/openbsd-src/share/misc/
H A Dairport1944 YMM:Fort McMurray, Alberta, Canada