+2017-04-07 Uros Bizjak <ubizjak@gmail.com>
+
+ Backport from mainline
+ 2017-04-06 Uros Bizjak <ubizjak@gmail.com>
+
+ PR target/79733
+ * config/i386/i386.c (ix86_expand_builtin)
+ <case IX86_BUILTIN_KORTEST{C,Z}16>: Determine insn operand
+ mode from insn data. Convert operands to insn operand mode.
+ Copy operands that don't satisfy insn predicate to a register.
+
2017-03-30 Peter Bergner <bergner@vnet.ibm.com>
Backport from mainline
case IX86_BUILTIN_KORTESTC16:
icode = CODE_FOR_kortestchi;
- mode0 = HImode;
- mode1 = CCCmode;
+ mode3 = CCCmode;
goto kortest;
case IX86_BUILTIN_KORTESTZ16:
icode = CODE_FOR_kortestzhi;
- mode0 = HImode;
- mode1 = CCZmode;
+ mode3 = CCZmode;
kortest:
arg0 = CALL_EXPR_ARG (exp, 0); /* Mask reg src1. */
op0 = expand_normal (arg0);
op1 = expand_normal (arg1);
- op0 = copy_to_reg (op0);
- op0 = simplify_gen_subreg (mode0, op0, GET_MODE (op0), 0);
- op1 = copy_to_reg (op1);
- op1 = simplify_gen_subreg (mode0, op1, GET_MODE (op1), 0);
+ mode0 = insn_data[icode].operand[0].mode;
+ mode1 = insn_data[icode].operand[1].mode;
+
+ if (GET_MODE (op0) != VOIDmode)
+ op0 = force_reg (GET_MODE (op0), op0);
+
+ op0 = gen_lowpart (mode0, op0);
+
+ if (!insn_data[icode].operand[0].predicate (op0, mode0))
+ op0 = copy_to_mode_reg (mode0, op0);
+
+ if (GET_MODE (op1) != VOIDmode)
+ op1 = force_reg (GET_MODE (op1), op1);
+
+ op1 = gen_lowpart (mode1, op1);
+
+ if (!insn_data[icode].operand[1].predicate (op1, mode1))
+ op1 = copy_to_mode_reg (mode1, op1);
target = gen_reg_rtx (QImode);
- emit_insn (gen_rtx_SET (mode0, target, const0_rtx));
/* Emit kortest. */
emit_insn (GEN_FCN (icode) (op0, op1));
/* And use setcc to return result from flags. */
ix86_expand_setcc (target, EQ,
- gen_rtx_REG (mode1, FLAGS_REG), const0_rtx);
+ gen_rtx_REG (mode3, FLAGS_REG), const0_rtx);
return target;
case IX86_BUILTIN_GATHERSIV2DF:
--- /dev/null
+/* PR target/79733 */
+/* { dg-do compile } */
+/* { dg-options "-O2 -mavx512f" } */
+
+typedef unsigned short __mmask16;
+
+extern __inline int
+__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
+_mm512_kortestc (__mmask16 __A, __mmask16 __B)
+{
+ return (__mmask16) __builtin_ia32_kortestchi ((__mmask16) __A,
+ (__mmask16) __B);
+}
+
+void
+avx512f_test ()
+{
+ volatile __mmask16 k1 = 0;
+ __mmask16 k2 = 0;
+ volatile short r;
+
+ r = _mm512_kortestc (k1, k2);
+}