}
/* Return the UNSPEC_CMLA* unspec for rotation amount ROT. */
-static int
+static unspec
unspec_cmla (int rot)
{
switch (rot)
}
/* Return the UNSPEC_FCMLA* unspec for rotation amount ROT. */
-static int
+static unspec
unspec_fcmla (int rot)
{
switch (rot)
}
/* Return the UNSPEC_COND_FCMLA* unspec for rotation amount ROT. */
-static int
+static unspec
unspec_cond_fcmla (int rot)
{
switch (rot)
/* Expand a call to svmla_lane or svmls_lane using floating-point unspec
UNSPEC. */
static rtx
-expand_mla_mls_lane (function_expander &e, int unspec)
+expand_mla_mls_lane (function_expander &e, unspec unspec)
{
/* Put the operands in the normal (fma ...) order, with the accumulator
last. This fits naturally since that's also the unprinted operand
class svac_impl : public function_base
{
public:
- constexpr svac_impl (int unspec) : m_unspec (unspec) {}
+ constexpr svac_impl (unspec unspec) : m_unspec (unspec) {}
gimple *
fold (gimple_folder &f) const override
}
/* The unspec code for the underlying comparison. */
- int m_unspec;
+ unspec m_unspec;
};
class svadda_impl : public function_base
{
machine_mode mode = GET_MODE_INNER (e.vector_mode (0));
e.args[2] = simplify_unary_operation (NOT, mode, e.args[2], mode);
- return e.map_to_rtx_codes (AND, AND, -1, -1);
+ return e.map_to_rtx_codes (AND, AND, UNSPEC_NONE, UNSPEC_NONE);
}
if (e.type_suffix_ids[0] == TYPE_SUFFIX_b)
class svbrk_binary_impl : public function_base
{
public:
- constexpr svbrk_binary_impl (int unspec) : m_unspec (unspec) {}
+ constexpr svbrk_binary_impl (unspec unspec) : m_unspec (unspec) {}
rtx
expand (function_expander &e) const override
}
/* The unspec code associated with the operation. */
- int m_unspec;
+ unspec m_unspec;
};
/* Implements svbrka and svbrkb. */
class svbrk_unary_impl : public function_base
{
public:
- constexpr svbrk_unary_impl (int unspec) : m_unspec (unspec) {}
+ constexpr svbrk_unary_impl (unspec unspec) : m_unspec (unspec) {}
rtx
expand (function_expander &e) const override
}
/* The unspec code associated with the operation. */
- int m_unspec;
+ unspec m_unspec;
};
class svcadd_impl : public function_base
class svclast_impl : public quiet<function_base>
{
public:
- constexpr svclast_impl (int unspec) : m_unspec (unspec) {}
+ constexpr svclast_impl (unspec unspec) : m_unspec (unspec) {}
gimple *
fold (gimple_folder &f) const override
}
/* The unspec code associated with the operation. */
- int m_unspec;
+ unspec m_unspec;
};
class svcmla_impl : public function_base
/* Make the operand order the same as the one used by the fma optabs,
with the accumulator last. */
e.rotate_inputs_left (1, 4);
- return e.map_to_unspecs (-1, -1, unspec_cond_fcmla (rot), 3);
+ return e.map_to_unspecs (UNSPEC_NONE, UNSPEC_NONE, unspec_cond_fcmla (rot), 3);
}
else
{
- int cmla = unspec_cmla (rot);
- return e.map_to_unspecs (cmla, cmla, -1);
+ unspec cmla = unspec_cmla (rot);
+ return e.map_to_unspecs (cmla, cmla, UNSPEC_NONE);
}
}
};
class svcmp_impl : public function_base
{
public:
- constexpr svcmp_impl (tree_code code, int unspec_for_fp)
+ constexpr svcmp_impl (tree_code code, unspec unspec_for_fp)
: m_code (code), m_unspec_for_fp (unspec_for_fp) {}
gimple *
tree_code m_code;
/* The unspec code to use for floating-point comparisons. */
- int m_unspec_for_fp;
+ unspec m_unspec_for_fp;
};
/* Implements svcmp<cc>_wide. */
class svcmp_wide_impl : public function_base
{
public:
- constexpr svcmp_wide_impl (tree_code code, int unspec_for_sint,
- int unspec_for_uint)
+ constexpr svcmp_wide_impl (tree_code code, unspec unspec_for_sint,
+ unspec unspec_for_uint)
: m_code (code), m_unspec_for_sint (unspec_for_sint),
m_unspec_for_uint (unspec_for_uint) {}
return e.use_exact_insn (icode);
}
- int unspec = (unsigned_p ? m_unspec_for_uint : m_unspec_for_sint);
+ unspec unspec = (unsigned_p ? m_unspec_for_uint : m_unspec_for_sint);
return e.use_exact_insn (code_for_aarch64_pred_cmp_wide (unspec, mode));
}
/* The unspec codes for signed and unsigned wide comparisons
respectively. */
- int m_unspec_for_sint;
- int m_unspec_for_uint;
+ unspec m_unspec_for_sint;
+ unspec m_unspec_for_uint;
};
class svcmpuo_impl : public quiet<function_base>
the source mode before the destination mode. */
if (e.type_suffix (1).integer_p)
{
- int unspec = (e.type_suffix (1).unsigned_p
- ? UNSPEC_COND_UCVTF
- : UNSPEC_COND_SCVTF);
+ unspec unspec = (e.type_suffix (1).unsigned_p
+ ? UNSPEC_COND_UCVTF
+ : UNSPEC_COND_SCVTF);
if (e.type_suffix (0).element_bytes <= e.type_suffix (1).element_bytes)
icode = (e.pred == PRED_x
? code_for_aarch64_sve_nonextend (unspec, mode1, mode0)
}
else
{
- int unspec = (!e.type_suffix (0).integer_p ? UNSPEC_COND_FCVT
- : e.type_suffix (0).unsigned_p ? UNSPEC_COND_FCVTZU
- : UNSPEC_COND_FCVTZS);
+ unspec unspec = (!e.type_suffix (0).integer_p ? UNSPEC_COND_FCVT
+ : e.type_suffix (0).unsigned_p ? UNSPEC_COND_FCVTZU
+ : UNSPEC_COND_FCVTZS);
if (e.type_suffix (0).element_bytes >= e.type_suffix (1).element_bytes)
icode = (e.pred == PRED_x
? code_for_aarch64_sve_nontrunc (unspec, mode1, mode0)
/* Use the same ordering as the dot_prod_optab, with the
accumulator last. */
e.rotate_inputs_left (0, 4);
- int unspec = unspec_for (e);
+ unspec unspec = unspec_for (e);
if (unspec == UNSPEC_FDOT)
icode = CODE_FOR_aarch64_fdot_prod_lanevnx4sfvnx8hf;
else
with an extra argument on the end. Take the inactive elements
from this extra argument. */
e.rotate_inputs_left (0, 4);
- return e.map_to_rtx_codes (AND, AND, -1, -1, 3);
+ return e.map_to_rtx_codes (AND, AND, UNSPEC_NONE, UNSPEC_NONE, 3);
}
machine_mode wide_mode = e.vector_mode (0);
class svlast_impl : public quiet<function_base>
{
public:
- constexpr svlast_impl (int unspec) : m_unspec (unspec) {}
+ constexpr svlast_impl (unspec unspec) : m_unspec (unspec) {}
bool is_lasta () const { return m_unspec == UNSPEC_LASTA; }
bool is_lastb () const { return m_unspec == UNSPEC_LASTB; }
}
/* The unspec code associated with the operation. */
- int m_unspec;
+ unspec m_unspec;
};
class svld1_impl : public full_width_access
class svldxf1_impl : public full_width_access
{
public:
- constexpr svldxf1_impl (int unspec) : m_unspec (unspec) {}
+ constexpr svldxf1_impl (unspec unspec) : m_unspec (unspec) {}
unsigned int
call_properties (const function_instance &) const override
}
/* The unspec associated with the load. */
- int m_unspec;
+ unspec m_unspec;
};
/* Implements extending contiguous forms of svldff1 and svldnf1. */
class svldxf1_extend_impl : public extending_load
{
public:
- constexpr svldxf1_extend_impl (type_suffix_index memory_type, int unspec)
+ constexpr svldxf1_extend_impl (type_suffix_index memory_type, unspec unspec)
: extending_load (memory_type), m_unspec (unspec) {}
unsigned int
}
/* The unspec associated with the load. */
- int m_unspec;
+ unspec m_unspec;
};
class svlen_impl : public quiet<function_base>
class svnot_impl : public rtx_code_function
{
public:
- constexpr svnot_impl () : rtx_code_function (NOT, NOT, -1) {}
+ constexpr svnot_impl () : rtx_code_function (NOT, NOT, UNSPEC_NONE) {}
rtx
expand (function_expander &e) const override
class svpfirst_svpnext_impl : public function_base
{
public:
- constexpr svpfirst_svpnext_impl (int unspec) : m_unspec (unspec) {}
+ constexpr svpfirst_svpnext_impl (unspec unspec) : m_unspec (unspec) {}
gimple *
fold (gimple_folder &f) const override
{
}
/* The unspec associated with the operation. */
- int m_unspec;
+ unspec m_unspec;
};
/* Implements contiguous forms of svprf[bhwd]. */
class svrint_impl : public function_base
{
public:
- constexpr svrint_impl (optab_tag optab, int cond_unspec)
+ constexpr svrint_impl (optab_tag optab, unspec cond_unspec)
: m_optab (optab), m_cond_unspec (cond_unspec)
{}
auto icode = direct_optab_handler (m_optab, e.tuple_mode (0));
return e.use_exact_insn (icode);
}
- return e.map_to_unspecs (-1, -1, m_cond_unspec);
+ return e.map_to_unspecs (UNSPEC_NONE, UNSPEC_NONE, m_cond_unspec);
}
optab_tag m_optab;
- int m_cond_unspec;
+ unspec m_cond_unspec;
};
class svsel_impl : public quiet<function_base>
/* Canonicalize subtractions of constants to additions. */
machine_mode mode = e.vector_mode (0);
if (e.try_negating_argument (2, mode))
- return e.map_to_rtx_codes (PLUS, PLUS, UNSPEC_COND_FADD, -1);
+ return e.map_to_rtx_codes (PLUS, PLUS, UNSPEC_COND_FADD, UNSPEC_NONE);
return rtx_code_function::expand (e);
}
expand (function_expander &e) const override
{
machine_mode mode = GET_MODE (e.args[0]);
- unsigned int unpacku = m_high_p ? UNSPEC_UNPACKUHI : UNSPEC_UNPACKULO;
- unsigned int unpacks = m_high_p ? UNSPEC_UNPACKSHI : UNSPEC_UNPACKSLO;
+ unspec unpacku = m_high_p ? UNSPEC_UNPACKUHI : UNSPEC_UNPACKULO;
+ unspec unpacks = m_high_p ? UNSPEC_UNPACKSHI : UNSPEC_UNPACKSLO;
insn_code icode;
if (GET_MODE_CLASS (mode) == MODE_VECTOR_BOOL)
icode = code_for_aarch64_sve_punpk_acle (unpacku);
else
{
- int unspec = e.type_suffix (0).unsigned_p ? unpacku : unpacks;
+ unspec unspec = e.type_suffix (0).unsigned_p ? unpacku : unpacks;
icode = code_for_aarch64_sve_unpk (unspec, unspec, mode);
}
return e.use_exact_insn (icode);
class svwhilelx_impl : public while_comparison
{
public:
- constexpr svwhilelx_impl (int unspec_for_sint, int unspec_for_uint, bool eq_p)
+ constexpr svwhilelx_impl (unspec unspec_for_sint, unspec unspec_for_uint, bool eq_p)
: while_comparison (unspec_for_sint, unspec_for_uint), m_eq_p (eq_p)
{}
expand (function_expander &e) const override
{
if (vectors_per_tuple (e) == 1)
- return e.map_to_unspecs (-1, -1, UNSPEC_COND_FSCALE);
+ return e.map_to_unspecs (UNSPEC_NONE, UNSPEC_NONE, UNSPEC_COND_FSCALE);
else
{
machine_mode mode = GET_MODE (e.args[0]);
FUNCTION (svandv, svandv_impl,)
FUNCTION (svasr, rtx_code_function, (ASHIFTRT, ASHIFTRT))
FUNCTION (svasr_wide, shift_wide, (ASHIFTRT, UNSPEC_ASHIFTRT_WIDE))
-FUNCTION (svasrd, unspec_based_function, (UNSPEC_ASRD, -1, -1))
+FUNCTION (svasrd, unspec_based_function, (UNSPEC_ASRD, UNSPEC_NONE, UNSPEC_NONE))
FUNCTION (svbfdot, fixed_insn_function, (CODE_FOR_aarch64_sve_bfdotvnx4sf))
FUNCTION (svbfdot_lane, fixed_insn_function,
(CODE_FOR_aarch64_sve_bfdot_lanevnx4sf))
FUNCTION (svdup_lane, svdup_lane_impl,)
FUNCTION (svdupq, svdupq_impl,)
FUNCTION (svdupq_lane, svdupq_lane_impl,)
-FUNCTION (sveor, rtx_code_function, (XOR, XOR, -1))
+FUNCTION (sveor, rtx_code_function, (XOR, XOR, UNSPEC_NONE))
FUNCTION (sveorv, sveorv_impl,)
-FUNCTION (svexpa, unspec_based_function, (-1, -1, UNSPEC_FEXPA))
+FUNCTION (svexpa, unspec_based_function, (UNSPEC_NONE, UNSPEC_NONE, UNSPEC_FEXPA))
FUNCTION (svexpand, svexpand_impl,)
FUNCTION (svext, QUIET_CODE_FOR_MODE0 (aarch64_sve_ext),)
FUNCTION (svextb, svext_bhw_impl, (QImode))
FUNCTION (svmul, svmul_impl,)
FUNCTION (svmul_lane, CODE_FOR_MODE0 (aarch64_mul_lane),)
FUNCTION (svmulh, unspec_based_function, (UNSPEC_SMUL_HIGHPART,
- UNSPEC_UMUL_HIGHPART, -1))
-FUNCTION (svmulx, unspec_based_function, (-1, -1, UNSPEC_COND_FMULX))
+ UNSPEC_UMUL_HIGHPART, UNSPEC_NONE))
+FUNCTION (svmulx, unspec_based_function, (UNSPEC_NONE, UNSPEC_NONE, UNSPEC_COND_FMULX))
FUNCTION (svnand, svnand_impl,)
FUNCTION (svneg, quiet<rtx_code_function>, (NEG, NEG, UNSPEC_COND_FNEG))
-FUNCTION (svnmad, unspec_based_function, (-1, -1, UNSPEC_COND_FNMLA))
-FUNCTION (svnmla, unspec_based_function_rotated, (-1, -1, UNSPEC_COND_FNMLA))
-FUNCTION (svnmls, unspec_based_function_rotated, (-1, -1, UNSPEC_COND_FNMLS))
-FUNCTION (svnmsb, unspec_based_function, (-1, -1, UNSPEC_COND_FNMLS))
+FUNCTION (svnmad, unspec_based_function, (UNSPEC_NONE, UNSPEC_NONE, UNSPEC_COND_FNMLA))
+FUNCTION (svnmla, unspec_based_function_rotated, (UNSPEC_NONE, UNSPEC_NONE, UNSPEC_COND_FNMLA))
+FUNCTION (svnmls, unspec_based_function_rotated, (UNSPEC_NONE, UNSPEC_NONE, UNSPEC_COND_FNMLS))
+FUNCTION (svnmsb, unspec_based_function, (UNSPEC_NONE, UNSPEC_NONE, UNSPEC_COND_FNMLS))
FUNCTION (svnor, svnor_impl,)
FUNCTION (svnot, svnot_impl,)
FUNCTION (svorn, svorn_impl,)
FUNCTION (svptest_last, svptest_impl, (LTU))
FUNCTION (svptrue, svptrue_impl,)
FUNCTION (svptrue_pat, svptrue_pat_impl,)
-FUNCTION (svqadd, rtx_code_function, (SS_PLUS, US_PLUS, -1))
+FUNCTION (svqadd, rtx_code_function, (SS_PLUS, US_PLUS, UNSPEC_NONE))
FUNCTION (svqdecb, svqdec_bhwd_impl, (QImode))
FUNCTION (svqdecb_pat, svqdec_bhwd_impl, (QImode))
FUNCTION (svqdecd, svqdec_bhwd_impl, (DImode))
FUNCTION (svqincp, svqdecp_svqincp_impl, (SS_PLUS, US_PLUS))
FUNCTION (svqincw, svqinc_bhwd_impl, (SImode))
FUNCTION (svqincw_pat, svqinc_bhwd_impl, (SImode))
-FUNCTION (svqsub, rtx_code_function, (SS_MINUS, US_MINUS, -1))
-FUNCTION (svrbit, rtx_code_function, (BITREVERSE, BITREVERSE, -1))
+FUNCTION (svqsub, rtx_code_function, (SS_MINUS, US_MINUS, UNSPEC_NONE))
+FUNCTION (svrbit, rtx_code_function, (BITREVERSE, BITREVERSE, UNSPEC_NONE))
FUNCTION (svrdffr, svrdffr_impl,)
-FUNCTION (svrecpe, unspec_based_function, (-1, UNSPEC_URECPE, UNSPEC_FRECPE))
-FUNCTION (svrecps, unspec_based_function, (-1, -1, UNSPEC_FRECPS))
-FUNCTION (svrecpx, unspec_based_function, (-1, -1, UNSPEC_COND_FRECPX))
+FUNCTION (svrecpe, unspec_based_function, (UNSPEC_NONE, UNSPEC_URECPE, UNSPEC_FRECPE))
+FUNCTION (svrecps, unspec_based_function, (UNSPEC_NONE, UNSPEC_NONE, UNSPEC_FRECPS))
+FUNCTION (svrecpx, unspec_based_function, (UNSPEC_NONE, UNSPEC_NONE, UNSPEC_COND_FRECPX))
FUNCTION (svreinterpret, svreinterpret_impl,)
FUNCTION (svrev, svrev_impl,)
-FUNCTION (svrevb, unspec_based_function, (UNSPEC_REVB, UNSPEC_REVB, -1))
-FUNCTION (svrevh, unspec_based_function, (UNSPEC_REVH, UNSPEC_REVH, -1))
-FUNCTION (svrevw, unspec_based_function, (UNSPEC_REVW, UNSPEC_REVW, -1))
+FUNCTION (svrevb, unspec_based_function, (UNSPEC_REVB, UNSPEC_REVB, UNSPEC_NONE))
+FUNCTION (svrevh, unspec_based_function, (UNSPEC_REVH, UNSPEC_REVH, UNSPEC_NONE))
+FUNCTION (svrevw, unspec_based_function, (UNSPEC_REVW, UNSPEC_REVW, UNSPEC_NONE))
FUNCTION (svrinta, svrint_impl, (round_optab, UNSPEC_COND_FRINTA))
FUNCTION (svrinti, svrint_impl, (nearbyint_optab, UNSPEC_COND_FRINTI))
FUNCTION (svrintm, svrint_impl, (floor_optab, UNSPEC_COND_FRINTM))
FUNCTION (svrintp, svrint_impl, (ceil_optab, UNSPEC_COND_FRINTP))
FUNCTION (svrintx, svrint_impl, (rint_optab, UNSPEC_COND_FRINTX))
FUNCTION (svrintz, svrint_impl, (btrunc_optab, UNSPEC_COND_FRINTZ))
-FUNCTION (svrsqrte, unspec_based_function, (-1, UNSPEC_RSQRTE, UNSPEC_RSQRTE))
-FUNCTION (svrsqrts, unspec_based_function, (-1, -1, UNSPEC_RSQRTS))
+FUNCTION (svrsqrte, unspec_based_function, (UNSPEC_NONE, UNSPEC_RSQRTE, UNSPEC_RSQRTE))
+FUNCTION (svrsqrts, unspec_based_function, (UNSPEC_NONE, UNSPEC_NONE, UNSPEC_RSQRTS))
FUNCTION (svscale, svscale_impl,)
FUNCTION (svsel, svsel_impl,)
FUNCTION (svset2, svset_impl, (2))
FUNCTION (svsub, svsub_impl,)
FUNCTION (svsubr, rtx_code_function_rotated, (MINUS, MINUS, UNSPEC_COND_FSUB))
FUNCTION (svsudot, svusdot_impl, (true))
-FUNCTION (svsudot_lane, svdotprod_lane_impl, (UNSPEC_SUDOT, -1, -1))
+FUNCTION (svsudot_lane, svdotprod_lane_impl, (UNSPEC_SUDOT, UNSPEC_NONE, UNSPEC_NONE))
FUNCTION (svtbl, quiet<unspec_based_uncond_function>, (UNSPEC_TBL, UNSPEC_TBL,
UNSPEC_TBL))
FUNCTION (svtmad, CODE_FOR_MODE0 (aarch64_sve_tmad),)
FUNCTION (svtrn2, svtrn_impl, (1))
FUNCTION (svtrn2q, unspec_based_function, (UNSPEC_TRN2Q, UNSPEC_TRN2Q,
UNSPEC_TRN2Q))
-FUNCTION (svtsmul, unspec_based_function, (-1, -1, UNSPEC_FTSMUL))
-FUNCTION (svtssel, unspec_based_function, (-1, -1, UNSPEC_FTSSEL))
+FUNCTION (svtsmul, unspec_based_function, (UNSPEC_NONE, UNSPEC_NONE, UNSPEC_FTSMUL))
+FUNCTION (svtssel, unspec_based_function, (UNSPEC_NONE, UNSPEC_NONE, UNSPEC_FTSSEL))
FUNCTION (svundef, svundef_impl, (1))
FUNCTION (svundef2, svundef_impl, (2))
FUNCTION (svundef3, svundef_impl, (3))
FUNCTION (svunpkhi, svunpk_impl, (true))
FUNCTION (svunpklo, svunpk_impl, (false))
FUNCTION (svusdot, svusdot_impl, (false))
-FUNCTION (svusdot_lane, svdotprod_lane_impl, (UNSPEC_USDOT, -1, -1))
-FUNCTION (svusmmla, unspec_based_add_function, (UNSPEC_USMATMUL, -1, -1))
+FUNCTION (svusdot_lane, svdotprod_lane_impl, (UNSPEC_USDOT, UNSPEC_NONE, UNSPEC_NONE))
+FUNCTION (svusmmla, unspec_based_add_function, (UNSPEC_USMATMUL, UNSPEC_NONE, UNSPEC_NONE))
FUNCTION (svuzp1, svuzp_impl, (0))
FUNCTION (svuzp1q, unspec_based_function, (UNSPEC_UZP1Q, UNSPEC_UZP1Q,
UNSPEC_UZP1Q))
public:
constexpr rtx_code_function_base (rtx_code code_for_sint,
rtx_code code_for_uint,
- int unspec_for_cond_fp = -1,
- int unspec_for_uncond_fp = -1)
+ unspec unspec_for_cond_fp = UNSPEC_NONE,
+ unspec unspec_for_uncond_fp = UNSPEC_NONE)
: m_code_for_sint (code_for_sint), m_code_for_uint (code_for_uint),
m_unspec_for_cond_fp (unspec_for_cond_fp),
m_unspec_for_uncond_fp (unspec_for_uncond_fp) {}
/* The UNSPEC_COND_* to use for floating-point operations. Can be -1
for functions that only operate on integers. */
- int m_unspec_for_cond_fp;
+ unspec m_unspec_for_cond_fp;
/* The UNSPEC_* to use for unpredicated floating-point operations.
Can be -1 if there is no such operation. */
- int m_unspec_for_uncond_fp;
+ unspec m_unspec_for_uncond_fp;
};
/* A function_base for functions that have an associated rtx code.
class unspec_based_function_base : public function_base
{
public:
- constexpr unspec_based_function_base (int unspec_for_sint,
- int unspec_for_uint,
- int unspec_for_fp,
- int unspec_for_mfp8 = -1,
+ constexpr unspec_based_function_base (unspec unspec_for_sint,
+ unspec unspec_for_uint,
+ unspec unspec_for_fp,
+ unspec unspec_for_mfp8 = UNSPEC_NONE,
unsigned int suffix_index = 0)
: m_unspec_for_sint (unspec_for_sint),
m_unspec_for_uint (unspec_for_uint),
{}
/* Return the unspec code to use for INSTANCE, based on type suffix 0. */
- int
+ unspec
unspec_for (const function_instance &instance) const
{
if (instance.fpm_mode == FPM_set)
/* The unspec code associated with signed-integer, unsigned-integer
and floating-point operations respectively. */
- int m_unspec_for_sint;
- int m_unspec_for_uint;
- int m_unspec_for_fp;
- int m_unspec_for_mfp8;
+ unspec m_unspec_for_sint;
+ unspec m_unspec_for_uint;
+ unspec m_unspec_for_fp;
+ unspec m_unspec_for_mfp8;
/* Which type suffix is used to choose between the unspecs. */
unsigned int m_suffix_index;
class cond_or_uncond_unspec_function : public function_base
{
public:
- constexpr cond_or_uncond_unspec_function (int cond_unspec, int uncond_unspec)
+ constexpr cond_or_uncond_unspec_function (unspec cond_unspec, unspec uncond_unspec)
: m_cond_unspec (cond_unspec), m_uncond_unspec (uncond_unspec) {}
rtx
/* The unspecs for the conditional and unconditional instructions,
respectively. */
- int m_cond_unspec;
- int m_uncond_unspec;
+ unspec m_cond_unspec;
+ unspec m_uncond_unspec;
};
/* General SME unspec-based functions, parameterized on the vector mode. */
public:
using parent = read_write_za<unspec_based_function_base>;
- constexpr sme_1mode_function (int unspec_for_sint, int unspec_for_uint,
- int unspec_for_fp)
- : parent (unspec_for_sint, unspec_for_uint, unspec_for_fp, -1, 1)
+ constexpr sme_1mode_function (unspec unspec_for_sint, unspec unspec_for_uint,
+ unspec unspec_for_fp)
+ : parent (unspec_for_sint, unspec_for_uint, unspec_for_fp, UNSPEC_NONE, 1)
{}
rtx
public:
using parent = read_write_za<unspec_based_function_base>;
- constexpr sme_2mode_function_t (int unspec_for_sint, int unspec_for_uint,
- int unspec_for_fp, int unspec_for_mfp8 = -1)
+ constexpr sme_2mode_function_t (unspec unspec_for_sint, unspec unspec_for_uint,
+ unspec unspec_for_fp, unspec unspec_for_mfp8 = UNSPEC_NONE)
: parent (unspec_for_sint, unspec_for_uint, unspec_for_fp, unspec_for_mfp8,
1)
{}
public:
using parent = read_write_za<unspec_based_function_base>;
- constexpr svvdot_half_impl (int unspec_for_sint, int unspec_for_uint,
- int unspec_for_fp, int unspec_for_mfp8)
+ constexpr svvdot_half_impl (unspec unspec_for_sint, unspec unspec_for_uint,
+ unspec unspec_for_fp, unspec unspec_for_mfp8)
: parent (unspec_for_sint, unspec_for_uint, unspec_for_fp, unspec_for_mfp8,
1)
{}
rtx
expand (function_expander &e) const override
{
- int unspec = unspec_for (e);
+ unspec unspec = unspec_for (e);
insn_code icode;
if (e.type_suffix (m_suffix_index).float_p
&& e.fpm_mode != FPM_set)
rtx
expand (function_expander &e) const override
{
- int unspec = unspec_for (e);
+ unspec unspec = unspec_for (e);
insn_code icode;
if (e.type_suffix (m_suffix_index).float_p
&& e.fpm_mode != FPM_set)
class binary_permute : public permute
{
public:
- constexpr binary_permute (int unspec) : m_unspec (unspec) {}
+ constexpr binary_permute (unspec unspec) : m_unspec (unspec) {}
rtx
expand (function_expander &e) const override
}
/* The unspec code associated with the operation. */
- int m_unspec;
+ unspec m_unspec;
};
/* A function that implements a x2 or x4 permute instruction. Both forms
class multireg_permute : public function_base
{
public:
- constexpr multireg_permute (int unspec) : m_unspec (unspec) {}
+ constexpr multireg_permute (unspec unspec) : m_unspec (unspec) {}
rtx
expand (function_expander &e) const override
}
/* The unspec associated with the permutation. */
- int m_unspec;
+ unspec m_unspec;
};
/* A function that has two type integer type suffixes, which might agree
class integer_conversion : public function_base
{
public:
- constexpr integer_conversion (int unspec_for_sint, int unspec_for_sintu,
- int unspec_for_uint, int unspec_for_uints)
+ constexpr integer_conversion (unspec unspec_for_sint, unspec unspec_for_sintu,
+ unspec unspec_for_uint, unspec unspec_for_uints)
: m_unspec_for_sint (unspec_for_sint),
m_unspec_for_sintu (unspec_for_sintu),
m_unspec_for_uint (unspec_for_uint),
{
machine_mode mode0 = e.vector_mode (0);
machine_mode mode1 = GET_MODE (e.args[0]);
- int unspec;
+ unspec unspec;
if (e.type_suffix (0).unsigned_p == e.type_suffix (1).unsigned_p)
unspec = (e.type_suffix (0).unsigned_p
? m_unspec_for_uint
}
/* The unspec for signed -> signed. */
- int m_unspec_for_sint;
+ unspec m_unspec_for_sint;
/* The unspec for signed -> unsigned. */
- int m_unspec_for_sintu;
+ unspec m_unspec_for_sintu;
/* The unspec for unsigned -> signed. */
- int m_unspec_for_uint;
+ unspec m_unspec_for_uint;
/* The unspec for unsigned -> unsigned. */
- int m_unspec_for_uints;
+ unspec m_unspec_for_uints;
};
/* A function_base for functions that reduce a vector to a scalar. */
class reduction : public function_base
{
public:
- constexpr reduction (int unspec)
+ constexpr reduction (unspec unspec)
: m_unspec_for_sint (unspec),
m_unspec_for_uint (unspec),
m_unspec_for_fp (unspec)
{}
- constexpr reduction (int unspec_for_sint, int unspec_for_uint,
- int unspec_for_fp)
+ constexpr reduction (unspec unspec_for_sint, unspec unspec_for_uint,
+ unspec unspec_for_fp)
: m_unspec_for_sint (unspec_for_sint),
m_unspec_for_uint (unspec_for_uint),
m_unspec_for_fp (unspec_for_fp)
expand (function_expander &e) const override
{
machine_mode mode = e.vector_mode (0);
- int unspec = (!e.type_suffix (0).integer_p ? m_unspec_for_fp
- : e.type_suffix (0).unsigned_p ? m_unspec_for_uint
- : m_unspec_for_sint);
+ unspec unspec = (!e.type_suffix (0).integer_p ? m_unspec_for_fp
+ : e.type_suffix (0).unsigned_p ? m_unspec_for_uint
+ : m_unspec_for_sint);
/* There's no distinction between SADDV and UADDV for 64-bit elements;
the signed versions only exist for narrower elements. */
if (GET_MODE_UNIT_BITSIZE (mode) == 64 && unspec == UNSPEC_SADDV)
/* The unspec code associated with signed-integer, unsigned-integer
and floating-point operations respectively. */
- int m_unspec_for_sint;
- int m_unspec_for_uint;
- int m_unspec_for_fp;
+ unspec m_unspec_for_sint;
+ unspec m_unspec_for_uint;
+ unspec m_unspec_for_fp;
};
/* A function_base for functions that shift narrower-than-64-bit values
if (aarch64_simd_shift_imm_p (shift, elem_mode, m_code == ASHIFT))
{
e.args.last () = shift;
- return e.map_to_rtx_codes (m_code, m_code, -1, -1);
+ return e.map_to_rtx_codes (m_code, m_code, UNSPEC_NONE, UNSPEC_NONE);
}
if (e.pred == PRED_x)
class while_comparison : public function_base
{
public:
- constexpr while_comparison (int unspec_for_sint, int unspec_for_uint)
+ constexpr while_comparison (unspec unspec_for_sint, unspec unspec_for_uint)
: m_unspec_for_sint (unspec_for_sint),
m_unspec_for_uint (unspec_for_uint)
{}
{
/* Suffix 0 determines the predicate mode, suffix 1 determines the
scalar mode and signedness. */
- int unspec = (e.type_suffix (1).unsigned_p
+ unspec unspec = (e.type_suffix (1).unsigned_p
? m_unspec_for_uint
: m_unspec_for_sint);
if (e.vectors_per_tuple () > 1)
/* The unspec codes associated with signed and unsigned operations
respectively. */
- int m_unspec_for_sint;
- int m_unspec_for_uint;
+ unspec m_unspec_for_sint;
+ unspec m_unspec_for_uint;
};
template<insn_code (*CODE_FOR_MODE) (machine_mode), unsigned int N>
namespace {
/* Return the UNSPEC_CDOT* unspec for rotation amount ROT. */
-static int
+static unspec
unspec_cdot (int rot)
{
switch (rot)
}
/* Return the UNSPEC_SQRDCMLAH* unspec for rotation amount ROT. */
-static int
+static unspec
unspec_sqrdcmlah (int rot)
{
switch (rot)
class svcvt_fp8_impl : public function_base
{
public:
- constexpr svcvt_fp8_impl (int unspec) : m_unspec (unspec) {}
+ constexpr svcvt_fp8_impl (unspec unspec) : m_unspec (unspec) {}
rtx
expand (function_expander &e) const override
return e.use_exact_insn (icode);
}
- int m_unspec;
+ unspec m_unspec;
};
class svcvtn_impl : public function_base
class svmatch_svnmatch_impl : public function_base
{
public:
- constexpr svmatch_svnmatch_impl (int unspec) : m_unspec (unspec) {}
+ constexpr svmatch_svnmatch_impl (unspec unspec) : m_unspec (unspec) {}
gimple *
fold (gimple_folder &f) const override
{
e.vector_mode (0)));
}
- int m_unspec;
+ unspec m_unspec;
};
/* Implements both svmovlb and svmovlt; the unspec parameters decide
/* Convert the rotation amount into a specific unspec. */
int rot = INTVAL (e.args.pop ());
if (rot == 90)
- return e.map_to_unspecs (UNSPEC_SQCADD90, -1, -1);
+ return e.map_to_unspecs (UNSPEC_SQCADD90, UNSPEC_NONE, UNSPEC_NONE);
if (rot == 270)
- return e.map_to_unspecs (UNSPEC_SQCADD270, -1, -1);
+ return e.map_to_unspecs (UNSPEC_SQCADD270, UNSPEC_NONE, UNSPEC_NONE);
gcc_unreachable ();
}
};
{
public:
constexpr svqrshl_impl ()
- : unspec_based_function (UNSPEC_SQRSHL, UNSPEC_UQRSHL, -1) {}
+ : unspec_based_function (UNSPEC_SQRSHL, UNSPEC_UQRSHL, UNSPEC_NONE) {}
gimple *
fold (gimple_folder &f) const override
{
public:
constexpr svqshl_impl ()
- : unspec_based_function (UNSPEC_SQSHL, UNSPEC_UQSHL, -1) {}
+ : unspec_based_function (UNSPEC_SQSHL, UNSPEC_UQSHL, UNSPEC_NONE) {}
gimple *
fold (gimple_folder &f) const override
{
public:
constexpr svrshl_impl ()
- : unspec_based_function (UNSPEC_SRSHL, UNSPEC_URSHL, -1) {}
+ : unspec_based_function (UNSPEC_SRSHL, UNSPEC_URSHL, UNSPEC_NONE) {}
gimple *
fold (gimple_folder &f) const override
machine_mode mode = e.vector_mode (0);
if (e.pred == PRED_x
&& aarch64_sve_sqadd_sqsub_immediate_p (mode, e.args[2], false))
- return e.map_to_rtx_codes (UNKNOWN, US_PLUS, -1, -1);
- return e.map_to_unspecs (-1, UNSPEC_USQADD, -1);
+ return e.map_to_rtx_codes (UNKNOWN, US_PLUS, UNSPEC_NONE, UNSPEC_NONE);
+ return e.map_to_unspecs (UNSPEC_NONE, UNSPEC_USQADD, UNSPEC_NONE);
}
};
if (e.pred == PRED_x
&& aarch64_sve_arith_immediate_p (mode, e.args[2], false))
return e.use_unpred_insn (code_for_aarch64_sve_suqadd_const (mode));
- return e.map_to_unspecs (UNSPEC_SUQADD, -1, -1);
+ return e.map_to_unspecs (UNSPEC_SUQADD, UNSPEC_NONE, UNSPEC_NONE);
}
};
class svwhilerw_svwhilewr_impl : public full_width_access
{
public:
- constexpr svwhilerw_svwhilewr_impl (int unspec) : m_unspec (unspec) {}
+ constexpr svwhilerw_svwhilewr_impl (unspec unspec) : m_unspec (unspec) {}
rtx
expand (function_expander &e) const override
return e.use_exact_insn (icode);
}
- int m_unspec;
+ unspec m_unspec;
};
/* Implements svzipq1 and svzipq2. */
class faminmaximpl : public function_base
{
public:
- constexpr faminmaximpl (int cond_unspec, int uncond_unspec)
+ constexpr faminmaximpl (unspec cond_unspec, unspec uncond_unspec)
: m_cond_unspec (cond_unspec), m_uncond_unspec (uncond_unspec) {}
rtx
/* The unspecs for the conditional and unconditional instructions,
respectively. */
- int m_cond_unspec;
- int m_uncond_unspec;
+ unspec m_cond_unspec;
+ unspec m_uncond_unspec;
};
} /* end anonymous namespace */
FUNCTION (svaba, svaba_impl,)
FUNCTION (svabalb, unspec_based_add_function, (UNSPEC_SABDLB,
- UNSPEC_UABDLB, -1))
+ UNSPEC_UABDLB, UNSPEC_NONE))
FUNCTION (svabalt, unspec_based_add_function, (UNSPEC_SABDLT,
- UNSPEC_UABDLT, -1))
-FUNCTION (svabdlb, unspec_based_function, (UNSPEC_SABDLB, UNSPEC_UABDLB, -1))
-FUNCTION (svabdlt, unspec_based_function, (UNSPEC_SABDLT, UNSPEC_UABDLT, -1))
-FUNCTION (svadalp, unspec_based_function, (UNSPEC_SADALP, UNSPEC_UADALP, -1))
-FUNCTION (svadclb, unspec_based_function, (-1, UNSPEC_ADCLB, -1))
-FUNCTION (svadclt, unspec_based_function, (-1, UNSPEC_ADCLT, -1))
-FUNCTION (svaddhnb, unspec_based_function, (UNSPEC_ADDHNB, UNSPEC_ADDHNB, -1))
-FUNCTION (svaddhnt, unspec_based_function, (UNSPEC_ADDHNT, UNSPEC_ADDHNT, -1))
-FUNCTION (svaddlb, unspec_based_function, (UNSPEC_SADDLB, UNSPEC_UADDLB, -1))
-FUNCTION (svaddlbt, unspec_based_function, (UNSPEC_SADDLBT, -1, -1))
-FUNCTION (svaddlt, unspec_based_function, (UNSPEC_SADDLT, UNSPEC_UADDLT, -1))
+ UNSPEC_UABDLT, UNSPEC_NONE))
+FUNCTION (svabdlb, unspec_based_function, (UNSPEC_SABDLB, UNSPEC_UABDLB, UNSPEC_NONE))
+FUNCTION (svabdlt, unspec_based_function, (UNSPEC_SABDLT, UNSPEC_UABDLT, UNSPEC_NONE))
+FUNCTION (svadalp, unspec_based_function, (UNSPEC_SADALP, UNSPEC_UADALP, UNSPEC_NONE))
+FUNCTION (svadclb, unspec_based_function, (UNSPEC_NONE, UNSPEC_ADCLB, UNSPEC_NONE))
+FUNCTION (svadclt, unspec_based_function, (UNSPEC_NONE, UNSPEC_ADCLT, UNSPEC_NONE))
+FUNCTION (svaddhnb, unspec_based_function, (UNSPEC_ADDHNB, UNSPEC_ADDHNB, UNSPEC_NONE))
+FUNCTION (svaddhnt, unspec_based_function, (UNSPEC_ADDHNT, UNSPEC_ADDHNT, UNSPEC_NONE))
+FUNCTION (svaddlb, unspec_based_function, (UNSPEC_SADDLB, UNSPEC_UADDLB, UNSPEC_NONE))
+FUNCTION (svaddlbt, unspec_based_function, (UNSPEC_SADDLBT, UNSPEC_NONE, UNSPEC_NONE))
+FUNCTION (svaddlt, unspec_based_function, (UNSPEC_SADDLT, UNSPEC_UADDLT, UNSPEC_NONE))
FUNCTION (svaddp, unspec_based_pred_function, (UNSPEC_ADDP, UNSPEC_ADDP,
UNSPEC_FADDP))
FUNCTION (svaddqv, reduction, (UNSPEC_ADDQV, UNSPEC_ADDQV, UNSPEC_FADDQV))
-FUNCTION (svaddwb, unspec_based_function, (UNSPEC_SADDWB, UNSPEC_UADDWB, -1))
-FUNCTION (svaddwt, unspec_based_function, (UNSPEC_SADDWT, UNSPEC_UADDWT, -1))
+FUNCTION (svaddwb, unspec_based_function, (UNSPEC_SADDWB, UNSPEC_UADDWB, UNSPEC_NONE))
+FUNCTION (svaddwt, unspec_based_function, (UNSPEC_SADDWT, UNSPEC_UADDWT, UNSPEC_NONE))
FUNCTION (svaesd, fixed_insn_function, (CODE_FOR_aarch64_sve2_aesd))
FUNCTION (svaese, fixed_insn_function, (CODE_FOR_aarch64_sve2_aese))
FUNCTION (svaesimc, fixed_insn_function, (CODE_FOR_aarch64_sve2_aesimc))
FUNCTION (svaesmc, fixed_insn_function, (CODE_FOR_aarch64_sve2_aesmc))
FUNCTION (svamax, faminmaximpl, (UNSPEC_COND_FAMAX, UNSPEC_FAMAX))
FUNCTION (svamin, faminmaximpl, (UNSPEC_COND_FAMIN, UNSPEC_FAMIN))
-FUNCTION (svandqv, reduction, (UNSPEC_ANDQV, UNSPEC_ANDQV, -1))
+FUNCTION (svandqv, reduction, (UNSPEC_ANDQV, UNSPEC_ANDQV, UNSPEC_NONE))
FUNCTION (svbcax, CODE_FOR_MODE0 (aarch64_sve2_bcax),)
-FUNCTION (svbdep, unspec_based_function, (UNSPEC_BDEP, UNSPEC_BDEP, -1))
-FUNCTION (svbext, unspec_based_function, (UNSPEC_BEXT, UNSPEC_BEXT, -1))
+FUNCTION (svbdep, unspec_based_function, (UNSPEC_BDEP, UNSPEC_BDEP, UNSPEC_NONE))
+FUNCTION (svbext, unspec_based_function, (UNSPEC_BEXT, UNSPEC_BEXT, UNSPEC_NONE))
FUNCTION (svbfmlslb, fixed_insn_function, (CODE_FOR_aarch64_sve_bfmlslbvnx4sf))
FUNCTION (svbfmlslb_lane, fixed_insn_function,
(CODE_FOR_aarch64_sve_bfmlslb_lanevnx4sf))
FUNCTION (svbfmlslt, fixed_insn_function, (CODE_FOR_aarch64_sve_bfmlsltvnx4sf))
FUNCTION (svbfmlslt_lane, fixed_insn_function,
(CODE_FOR_aarch64_sve_bfmlslt_lanevnx4sf))
-FUNCTION (svbgrp, unspec_based_function, (UNSPEC_BGRP, UNSPEC_BGRP, -1))
+FUNCTION (svbgrp, unspec_based_function, (UNSPEC_BGRP, UNSPEC_BGRP, UNSPEC_NONE))
FUNCTION (svbsl, CODE_FOR_MODE0 (aarch64_sve2_bsl),)
FUNCTION (svbsl1n, CODE_FOR_MODE0 (aarch64_sve2_bsl1n),)
FUNCTION (svbsl2n, CODE_FOR_MODE0 (aarch64_sve2_bsl2n),)
FUNCTION (svcvtl2, svcvt_fp8_impl, (UNSPEC_F2CVTL))
FUNCTION (svcvtlt1, svcvt_fp8_impl, (UNSPEC_F1CVTLT))
FUNCTION (svcvtlt2, svcvt_fp8_impl, (UNSPEC_F2CVTLT))
-FUNCTION (svcvtlt, unspec_based_function, (-1, -1, UNSPEC_COND_FCVTLT))
+FUNCTION (svcvtlt, unspec_based_function, (UNSPEC_NONE, UNSPEC_NONE, UNSPEC_COND_FCVTLT))
FUNCTION (svcvtn, svcvtn_impl,)
FUNCTION (svcvtnb, fixed_insn_function, (CODE_FOR_aarch64_sve2_fp8_cvtnbvnx16qi))
-FUNCTION (svcvtx, unspec_based_function, (-1, -1, UNSPEC_COND_FCVTX))
+FUNCTION (svcvtx, unspec_based_function, (UNSPEC_NONE, UNSPEC_NONE, UNSPEC_COND_FCVTX))
FUNCTION (svcvtxnt, NARROWING_TOP_CONVERT1 (aarch64_sve2_cvtxnt),)
FUNCTION (svcvtt, svcvtt_impl,)
FUNCTION (svcvtb, svcvtb_impl,)
FUNCTION (svdup_laneq, svdup_laneq_impl,)
FUNCTION (sveor3, CODE_FOR_MODE0 (aarch64_sve2_eor3),)
-FUNCTION (sveorbt, unspec_based_function, (UNSPEC_EORBT, UNSPEC_EORBT, -1))
-FUNCTION (sveorqv, reduction, (UNSPEC_EORQV, UNSPEC_EORQV, -1))
-FUNCTION (sveortb, unspec_based_function, (UNSPEC_EORTB, UNSPEC_EORTB, -1))
+FUNCTION (sveorbt, unspec_based_function, (UNSPEC_EORBT, UNSPEC_EORBT, UNSPEC_NONE))
+FUNCTION (sveorqv, reduction, (UNSPEC_EORQV, UNSPEC_EORQV, UNSPEC_NONE))
+FUNCTION (sveortb, unspec_based_function, (UNSPEC_EORTB, UNSPEC_EORTB, UNSPEC_NONE))
FUNCTION (svextq, svextq_impl,)
FUNCTION (svfirstp, svfirst_lastp_impl, (true))
-FUNCTION (svhadd, unspec_based_function, (UNSPEC_SHADD, UNSPEC_UHADD, -1))
-FUNCTION (svhsub, unspec_based_function, (UNSPEC_SHSUB, UNSPEC_UHSUB, -1))
+FUNCTION (svhadd, unspec_based_function, (UNSPEC_SHADD, UNSPEC_UHADD, UNSPEC_NONE))
+FUNCTION (svhsub, unspec_based_function, (UNSPEC_SHSUB, UNSPEC_UHSUB, UNSPEC_NONE))
FUNCTION (svhistcnt, CODE_FOR_MODE0 (aarch64_sve2_histcnt),)
FUNCTION (svhistseg, CODE_FOR_MODE0 (aarch64_sve2_histseg),)
FUNCTION (svhsubr, unspec_based_function_rotated, (UNSPEC_SHSUB,
- UNSPEC_UHSUB, -1))
+ UNSPEC_UHSUB, UNSPEC_NONE))
FUNCTION (svlastp, svfirst_lastp_impl, (false))
FUNCTION (svld1q_gather, svld1q_gather_impl,)
FUNCTION (svld1udq, svld1uxq_impl, (VNx1DImode))
FUNCTION (svldnt1ub_gather, svldnt1_gather_extend_impl, (TYPE_SUFFIX_u8))
FUNCTION (svldnt1uh_gather, svldnt1_gather_extend_impl, (TYPE_SUFFIX_u16))
FUNCTION (svldnt1uw_gather, svldnt1_gather_extend_impl, (TYPE_SUFFIX_u32))
-FUNCTION (svlogb, unspec_based_function, (-1, -1, UNSPEC_COND_FLOGB))
+FUNCTION (svlogb, unspec_based_function, (UNSPEC_NONE, UNSPEC_NONE, UNSPEC_COND_FLOGB))
FUNCTION (svmatch, svmatch_svnmatch_impl, (UNSPEC_MATCH))
-FUNCTION (svmaxnmp, unspec_based_pred_function, (-1, -1, UNSPEC_FMAXNMP))
-FUNCTION (svmaxnmqv, reduction, (-1, -1, UNSPEC_FMAXNMQV))
+FUNCTION (svmaxnmp, unspec_based_pred_function, (UNSPEC_NONE, UNSPEC_NONE, UNSPEC_FMAXNMP))
+FUNCTION (svmaxnmqv, reduction, (UNSPEC_NONE, UNSPEC_NONE, UNSPEC_FMAXNMQV))
FUNCTION (svmaxp, unspec_based_pred_function, (UNSPEC_SMAXP, UNSPEC_UMAXP,
UNSPEC_FMAXP))
FUNCTION (svmaxqv, reduction, (UNSPEC_SMAXQV, UNSPEC_UMAXQV, UNSPEC_FMAXQV))
-FUNCTION (svminnmp, unspec_based_pred_function, (-1, -1, UNSPEC_FMINNMP))
-FUNCTION (svminnmqv, reduction, (-1, -1, UNSPEC_FMINNMQV))
+FUNCTION (svminnmp, unspec_based_pred_function, (UNSPEC_NONE, UNSPEC_NONE, UNSPEC_FMINNMP))
+FUNCTION (svminnmqv, reduction, (UNSPEC_NONE, UNSPEC_NONE, UNSPEC_FMINNMQV))
FUNCTION (svminp, unspec_based_pred_function, (UNSPEC_SMINP, UNSPEC_UMINP,
UNSPEC_FMINP))
FUNCTION (svminqv, reduction, (UNSPEC_SMINQV, UNSPEC_UMINQV, UNSPEC_FMINQV))
(UNSPEC_SMULLB, UNSPEC_UMULLB, UNSPEC_FMLALB,
UNSPEC_FMLALB_FP8))
FUNCTION (svmlallbb_lane, unspec_based_mla_lane_function,
- (-1, -1, -1, UNSPEC_FMLALLBB_FP8))
+ (UNSPEC_NONE, UNSPEC_NONE, UNSPEC_NONE, UNSPEC_FMLALLBB_FP8))
FUNCTION (svmlallbb, unspec_based_mla_function,
- (-1, -1, -1, UNSPEC_FMLALLBB_FP8))
+ (UNSPEC_NONE, UNSPEC_NONE, UNSPEC_NONE, UNSPEC_FMLALLBB_FP8))
FUNCTION (svmlallbt_lane, unspec_based_mla_lane_function,
- (-1, -1, -1, UNSPEC_FMLALLBT_FP8))
+ (UNSPEC_NONE, UNSPEC_NONE, UNSPEC_NONE, UNSPEC_FMLALLBT_FP8))
FUNCTION (svmlallbt, unspec_based_mla_function,
- (-1, -1, -1, UNSPEC_FMLALLBT_FP8))
+ (UNSPEC_NONE, UNSPEC_NONE, UNSPEC_NONE, UNSPEC_FMLALLBT_FP8))
FUNCTION (svmlalltb_lane, unspec_based_mla_lane_function,
- (-1, -1, -1, UNSPEC_FMLALLTB_FP8))
+ (UNSPEC_NONE, UNSPEC_NONE, UNSPEC_NONE, UNSPEC_FMLALLTB_FP8))
FUNCTION (svmlalltb, unspec_based_mla_function,
- (-1, -1, -1, UNSPEC_FMLALLTB_FP8))
+ (UNSPEC_NONE, UNSPEC_NONE, UNSPEC_NONE, UNSPEC_FMLALLTB_FP8))
FUNCTION (svmlalltt_lane, unspec_based_mla_lane_function,
- (-1, -1, -1, UNSPEC_FMLALLTT_FP8))
+ (UNSPEC_NONE, UNSPEC_NONE, UNSPEC_NONE, UNSPEC_FMLALLTT_FP8))
FUNCTION (svmlalltt, unspec_based_mla_function,
- (-1, -1, -1, UNSPEC_FMLALLTT_FP8))
+ (UNSPEC_NONE, UNSPEC_NONE, UNSPEC_NONE, UNSPEC_FMLALLTT_FP8))
FUNCTION (svmlalt_lane, unspec_based_mla_lane_function,
(UNSPEC_SMULLT, UNSPEC_UMULLT, UNSPEC_FMLALT,
UNSPEC_FMLALT_FP8))
FUNCTION (svmlslt_lane, unspec_based_mls_lane_function, (UNSPEC_SMULLT,
UNSPEC_UMULLT,
UNSPEC_FMLSLT))
-FUNCTION (svmovlb, svmovl_lb_impl, (UNSPEC_SSHLLB, UNSPEC_USHLLB, -1))
-FUNCTION (svmovlt, svmovl_lb_impl, (UNSPEC_SSHLLT, UNSPEC_USHLLT, -1))
-FUNCTION (svmullb, unspec_based_function, (UNSPEC_SMULLB, UNSPEC_UMULLB, -1))
+FUNCTION (svmovlb, svmovl_lb_impl, (UNSPEC_SSHLLB, UNSPEC_USHLLB, UNSPEC_NONE))
+FUNCTION (svmovlt, svmovl_lb_impl, (UNSPEC_SSHLLT, UNSPEC_USHLLT, UNSPEC_NONE))
+FUNCTION (svmullb, unspec_based_function, (UNSPEC_SMULLB, UNSPEC_UMULLB, UNSPEC_NONE))
FUNCTION (svmullb_lane, unspec_based_lane_function, (UNSPEC_SMULLB,
- UNSPEC_UMULLB, -1))
-FUNCTION (svmullt, unspec_based_function, (UNSPEC_SMULLT, UNSPEC_UMULLT, -1))
+ UNSPEC_UMULLB, UNSPEC_NONE))
+FUNCTION (svmullt, unspec_based_function, (UNSPEC_SMULLT, UNSPEC_UMULLT, UNSPEC_NONE))
FUNCTION (svmullt_lane, unspec_based_lane_function, (UNSPEC_SMULLT,
- UNSPEC_UMULLT, -1))
+ UNSPEC_UMULLT, UNSPEC_NONE))
FUNCTION (svnbsl, CODE_FOR_MODE0 (aarch64_sve2_nbsl),)
FUNCTION (svnmatch, svmatch_svnmatch_impl, (UNSPEC_NMATCH))
-FUNCTION (svorqv, reduction, (UNSPEC_ORQV, UNSPEC_ORQV, -1))
+FUNCTION (svorqv, reduction, (UNSPEC_ORQV, UNSPEC_ORQV, UNSPEC_NONE))
FUNCTION (svpext_lane, svpext_lane_impl,)
FUNCTION (svpmov, svpmov_impl,)
FUNCTION (svpmov_lane, svpmov_lane_impl,)
FUNCTION (svpmul, CODE_FOR_MODE0 (aarch64_sve2_pmul),)
-FUNCTION (svpmullb, unspec_based_function, (-1, UNSPEC_PMULLB, -1))
-FUNCTION (svpmullb_pair, unspec_based_function, (-1, UNSPEC_PMULLB_PAIR, -1))
-FUNCTION (svpmullt, unspec_based_function, (-1, UNSPEC_PMULLT, -1))
-FUNCTION (svpmullt_pair, unspec_based_function, (-1, UNSPEC_PMULLT_PAIR, -1))
+FUNCTION (svpmullb, unspec_based_function, (UNSPEC_NONE, UNSPEC_PMULLB, UNSPEC_NONE))
+FUNCTION (svpmullb_pair, unspec_based_function, (UNSPEC_NONE, UNSPEC_PMULLB_PAIR, UNSPEC_NONE))
+FUNCTION (svpmullt, unspec_based_function, (UNSPEC_NONE, UNSPEC_PMULLT, UNSPEC_NONE))
+FUNCTION (svpmullt_pair, unspec_based_function, (UNSPEC_NONE, UNSPEC_PMULLT_PAIR, UNSPEC_NONE))
FUNCTION (svpsel_lane, svpsel_lane_impl,)
-FUNCTION (svqabs, rtx_code_function, (SS_ABS, UNKNOWN, UNKNOWN))
+FUNCTION (svqabs, rtx_code_function, (SS_ABS, UNKNOWN, UNSPEC_NONE))
FUNCTION (svqcadd, svqcadd_impl,)
FUNCTION (svqcvt, integer_conversion, (UNSPEC_SQCVT, UNSPEC_SQCVTU,
- UNSPEC_UQCVT, -1))
+ UNSPEC_UQCVT, UNSPEC_NONE))
FUNCTION (svqcvtn, integer_conversion, (UNSPEC_SQCVTN, UNSPEC_SQCVTUN,
- UNSPEC_UQCVTN, -1))
-FUNCTION (svqdmlalb, unspec_based_qadd_function, (UNSPEC_SQDMULLB, -1, -1))
+ UNSPEC_UQCVTN, UNSPEC_NONE))
+FUNCTION (svqdmlalb, unspec_based_qadd_function, (UNSPEC_SQDMULLB, UNSPEC_NONE, UNSPEC_NONE))
FUNCTION (svqdmlalb_lane, unspec_based_qadd_lane_function, (UNSPEC_SQDMULLB,
- -1, -1))
-FUNCTION (svqdmlalbt, unspec_based_qadd_function, (UNSPEC_SQDMULLBT, -1, -1))
-FUNCTION (svqdmlalt, unspec_based_qadd_function, (UNSPEC_SQDMULLT, -1, -1))
+ UNSPEC_NONE, UNSPEC_NONE))
+FUNCTION (svqdmlalbt, unspec_based_qadd_function, (UNSPEC_SQDMULLBT, UNSPEC_NONE, UNSPEC_NONE))
+FUNCTION (svqdmlalt, unspec_based_qadd_function, (UNSPEC_SQDMULLT, UNSPEC_NONE, UNSPEC_NONE))
FUNCTION (svqdmlalt_lane, unspec_based_qadd_lane_function, (UNSPEC_SQDMULLT,
- -1, -1))
-FUNCTION (svqdmlslb, unspec_based_qsub_function, (UNSPEC_SQDMULLB, -1, -1))
+ UNSPEC_NONE, UNSPEC_NONE))
+FUNCTION (svqdmlslb, unspec_based_qsub_function, (UNSPEC_SQDMULLB, UNSPEC_NONE, UNSPEC_NONE))
FUNCTION (svqdmlslb_lane, unspec_based_qsub_lane_function, (UNSPEC_SQDMULLB,
- -1, -1))
-FUNCTION (svqdmlslbt, unspec_based_qsub_function, (UNSPEC_SQDMULLBT, -1, -1))
-FUNCTION (svqdmlslt, unspec_based_qsub_function, (UNSPEC_SQDMULLT, -1, -1))
+ UNSPEC_NONE, UNSPEC_NONE))
+FUNCTION (svqdmlslbt, unspec_based_qsub_function, (UNSPEC_SQDMULLBT, UNSPEC_NONE, UNSPEC_NONE))
+FUNCTION (svqdmlslt, unspec_based_qsub_function, (UNSPEC_SQDMULLT, UNSPEC_NONE, UNSPEC_NONE))
FUNCTION (svqdmlslt_lane, unspec_based_qsub_lane_function, (UNSPEC_SQDMULLT,
- -1, -1))
-FUNCTION (svqdmulh, unspec_based_function, (UNSPEC_SQDMULH, -1, -1))
-FUNCTION (svqdmulh_lane, unspec_based_lane_function, (UNSPEC_SQDMULH, -1, -1))
-FUNCTION (svqdmullb, unspec_based_function, (UNSPEC_SQDMULLB, -1, -1))
+ UNSPEC_NONE, UNSPEC_NONE))
+FUNCTION (svqdmulh, unspec_based_function, (UNSPEC_SQDMULH, UNSPEC_NONE, UNSPEC_NONE))
+FUNCTION (svqdmulh_lane, unspec_based_lane_function, (UNSPEC_SQDMULH, UNSPEC_NONE, UNSPEC_NONE))
+FUNCTION (svqdmullb, unspec_based_function, (UNSPEC_SQDMULLB, UNSPEC_NONE, UNSPEC_NONE))
FUNCTION (svqdmullb_lane, unspec_based_lane_function, (UNSPEC_SQDMULLB,
- -1, -1))
-FUNCTION (svqdmullt, unspec_based_function, (UNSPEC_SQDMULLT, -1, -1))
+ UNSPEC_NONE, UNSPEC_NONE))
+FUNCTION (svqdmullt, unspec_based_function, (UNSPEC_SQDMULLT, UNSPEC_NONE, UNSPEC_NONE))
FUNCTION (svqdmullt_lane, unspec_based_lane_function, (UNSPEC_SQDMULLT,
- -1, -1))
-FUNCTION (svqneg, rtx_code_function, (SS_NEG, UNKNOWN, UNKNOWN))
+ UNSPEC_NONE, UNSPEC_NONE))
+FUNCTION (svqneg, rtx_code_function, (SS_NEG, UNKNOWN, UNSPEC_NONE))
FUNCTION (svqrdcmlah, svqrdcmlah_impl,)
FUNCTION (svqrdcmlah_lane, svqrdcmlah_lane_impl,)
-FUNCTION (svqrdmlah, unspec_based_function, (UNSPEC_SQRDMLAH, -1, -1))
+FUNCTION (svqrdmlah, unspec_based_function, (UNSPEC_SQRDMLAH, UNSPEC_NONE, UNSPEC_NONE))
FUNCTION (svqrdmlah_lane, unspec_based_lane_function, (UNSPEC_SQRDMLAH,
- -1, -1))
-FUNCTION (svqrdmlsh, unspec_based_function, (UNSPEC_SQRDMLSH, -1, -1))
+ UNSPEC_NONE, UNSPEC_NONE))
+FUNCTION (svqrdmlsh, unspec_based_function, (UNSPEC_SQRDMLSH, UNSPEC_NONE, UNSPEC_NONE))
FUNCTION (svqrdmlsh_lane, unspec_based_lane_function, (UNSPEC_SQRDMLSH,
- -1, -1))
-FUNCTION (svqrdmulh, unspec_based_function, (UNSPEC_SQRDMULH, -1, -1))
+ UNSPEC_NONE, UNSPEC_NONE))
+FUNCTION (svqrdmulh, unspec_based_function, (UNSPEC_SQRDMULH, UNSPEC_NONE, UNSPEC_NONE))
FUNCTION (svqrdmulh_lane, unspec_based_lane_function, (UNSPEC_SQRDMULH,
- -1, -1))
+ UNSPEC_NONE, UNSPEC_NONE))
FUNCTION (svqrshl, svqrshl_impl,)
FUNCTION (svqrshr, unspec_based_uncond_function, (UNSPEC_SQRSHR,
- UNSPEC_UQRSHR, -1, -1, 1))
+ UNSPEC_UQRSHR, UNSPEC_NONE, UNSPEC_NONE, 1))
FUNCTION (svqrshrn, unspec_based_uncond_function, (UNSPEC_SQRSHRN,
- UNSPEC_UQRSHRN, -1, -1, 1))
+ UNSPEC_UQRSHRN, UNSPEC_NONE, UNSPEC_NONE, 1))
FUNCTION (svqrshrnb, unspec_based_function, (UNSPEC_SQRSHRNB,
- UNSPEC_UQRSHRNB, -1))
+ UNSPEC_UQRSHRNB, UNSPEC_NONE))
FUNCTION (svqrshrnt, unspec_based_function, (UNSPEC_SQRSHRNT,
- UNSPEC_UQRSHRNT, -1))
-FUNCTION (svqrshru, unspec_based_uncond_function, (UNSPEC_SQRSHRU, -1, -1, -1, 1))
-FUNCTION (svqrshrun, unspec_based_uncond_function, (UNSPEC_SQRSHRUN, -1, -1, -1, 1))
-FUNCTION (svqrshrunb, unspec_based_function, (UNSPEC_SQRSHRUNB, -1, -1))
-FUNCTION (svqrshrunt, unspec_based_function, (UNSPEC_SQRSHRUNT, -1, -1))
+ UNSPEC_UQRSHRNT, UNSPEC_NONE))
+FUNCTION (svqrshru, unspec_based_uncond_function, (UNSPEC_SQRSHRU, UNSPEC_NONE, UNSPEC_NONE, UNSPEC_NONE, 1))
+FUNCTION (svqrshrun, unspec_based_uncond_function, (UNSPEC_SQRSHRUN, UNSPEC_NONE, UNSPEC_NONE, UNSPEC_NONE, 1))
+FUNCTION (svqrshrunb, unspec_based_function, (UNSPEC_SQRSHRUNB, UNSPEC_NONE, UNSPEC_NONE))
+FUNCTION (svqrshrunt, unspec_based_function, (UNSPEC_SQRSHRUNT, UNSPEC_NONE, UNSPEC_NONE))
FUNCTION (svqshl, svqshl_impl,)
-FUNCTION (svqshlu, unspec_based_function, (UNSPEC_SQSHLU, -1, -1))
+FUNCTION (svqshlu, unspec_based_function, (UNSPEC_SQSHLU, UNSPEC_NONE, UNSPEC_NONE))
FUNCTION (svqshrnb, unspec_based_function, (UNSPEC_SQSHRNB,
- UNSPEC_UQSHRNB, -1))
+ UNSPEC_UQSHRNB, UNSPEC_NONE))
FUNCTION (svqshrnt, unspec_based_function, (UNSPEC_SQSHRNT,
- UNSPEC_UQSHRNT, -1))
-FUNCTION (svqshrunb, unspec_based_function, (UNSPEC_SQSHRUNB, -1, -1))
-FUNCTION (svqshrunt, unspec_based_function, (UNSPEC_SQSHRUNT, -1, -1))
-FUNCTION (svqsubr, rtx_code_function_rotated, (SS_MINUS, US_MINUS, -1))
-FUNCTION (svqxtnb, unspec_based_function, (UNSPEC_SQXTNB, UNSPEC_UQXTNB, -1))
-FUNCTION (svqxtnt, unspec_based_function, (UNSPEC_SQXTNT, UNSPEC_UQXTNT, -1))
-FUNCTION (svqxtunb, unspec_based_function, (UNSPEC_SQXTUNB, -1, -1))
-FUNCTION (svqxtunt, unspec_based_function, (UNSPEC_SQXTUNT, -1, -1))
+ UNSPEC_UQSHRNT, UNSPEC_NONE))
+FUNCTION (svqshrunb, unspec_based_function, (UNSPEC_SQSHRUNB, UNSPEC_NONE, UNSPEC_NONE))
+FUNCTION (svqshrunt, unspec_based_function, (UNSPEC_SQSHRUNT, UNSPEC_NONE, UNSPEC_NONE))
+FUNCTION (svqsubr, rtx_code_function_rotated, (SS_MINUS, US_MINUS, UNSPEC_NONE))
+FUNCTION (svqxtnb, unspec_based_function, (UNSPEC_SQXTNB, UNSPEC_UQXTNB, UNSPEC_NONE))
+FUNCTION (svqxtnt, unspec_based_function, (UNSPEC_SQXTNT, UNSPEC_UQXTNT, UNSPEC_NONE))
+FUNCTION (svqxtunb, unspec_based_function, (UNSPEC_SQXTUNB, UNSPEC_NONE, UNSPEC_NONE))
+FUNCTION (svqxtunt, unspec_based_function, (UNSPEC_SQXTUNT, UNSPEC_NONE, UNSPEC_NONE))
FUNCTION (svraddhnb, unspec_based_function, (UNSPEC_RADDHNB,
- UNSPEC_RADDHNB, -1))
+ UNSPEC_RADDHNB, UNSPEC_NONE))
FUNCTION (svraddhnt, unspec_based_function, (UNSPEC_RADDHNT,
- UNSPEC_RADDHNT, -1))
+ UNSPEC_RADDHNT, UNSPEC_NONE))
FUNCTION (svrax1, fixed_insn_function, (CODE_FOR_aarch64_sve2_rax1))
FUNCTION (svrevd, unspec_based_function, (UNSPEC_REVD, UNSPEC_REVD,
UNSPEC_REVD))
-FUNCTION (svrhadd, unspec_based_function, (UNSPEC_SRHADD, UNSPEC_URHADD, -1))
-FUNCTION (svrint32x, unspec_based_function, (-1, -1, UNSPEC_FRINT32X))
-FUNCTION (svrint32z, unspec_based_function, (-1, -1, UNSPEC_FRINT32Z))
-FUNCTION (svrint64x, unspec_based_function, (-1, -1, UNSPEC_FRINT64X))
-FUNCTION (svrint64z, unspec_based_function, (-1, -1, UNSPEC_FRINT64Z))
+FUNCTION (svrhadd, unspec_based_function, (UNSPEC_SRHADD, UNSPEC_URHADD, UNSPEC_NONE))
+FUNCTION (svrint32x, unspec_based_function, (UNSPEC_NONE, UNSPEC_NONE, UNSPEC_FRINT32X))
+FUNCTION (svrint32z, unspec_based_function, (UNSPEC_NONE, UNSPEC_NONE, UNSPEC_FRINT32Z))
+FUNCTION (svrint64x, unspec_based_function, (UNSPEC_NONE, UNSPEC_NONE, UNSPEC_FRINT64X))
+FUNCTION (svrint64z, unspec_based_function, (UNSPEC_NONE, UNSPEC_NONE, UNSPEC_FRINT64Z))
FUNCTION (svrshl, svrshl_impl,)
-FUNCTION (svrshr, unspec_based_function, (UNSPEC_SRSHR, UNSPEC_URSHR, -1))
-FUNCTION (svrshrnb, unspec_based_function, (UNSPEC_RSHRNB, UNSPEC_RSHRNB, -1))
-FUNCTION (svrshrnt, unspec_based_function, (UNSPEC_RSHRNT, UNSPEC_RSHRNT, -1))
-FUNCTION (svrsra, unspec_based_add_function, (UNSPEC_SRSHR, UNSPEC_URSHR, -1))
+FUNCTION (svrshr, unspec_based_function, (UNSPEC_SRSHR, UNSPEC_URSHR, UNSPEC_NONE))
+FUNCTION (svrshrnb, unspec_based_function, (UNSPEC_RSHRNB, UNSPEC_RSHRNB, UNSPEC_NONE))
+FUNCTION (svrshrnt, unspec_based_function, (UNSPEC_RSHRNT, UNSPEC_RSHRNT, UNSPEC_NONE))
+FUNCTION (svrsra, unspec_based_add_function, (UNSPEC_SRSHR, UNSPEC_URSHR, UNSPEC_NONE))
FUNCTION (svrsubhnb, unspec_based_function, (UNSPEC_RSUBHNB,
- UNSPEC_RSUBHNB, -1))
+ UNSPEC_RSUBHNB, UNSPEC_NONE))
FUNCTION (svrsubhnt, unspec_based_function, (UNSPEC_RSUBHNT,
- UNSPEC_RSUBHNT, -1))
-FUNCTION (svsbclb, unspec_based_function, (-1, UNSPEC_SBCLB, -1))
-FUNCTION (svsbclt, unspec_based_function, (-1, UNSPEC_SBCLT, -1))
-FUNCTION (svshllb, unspec_based_function, (UNSPEC_SSHLLB, UNSPEC_USHLLB, -1))
-FUNCTION (svshllt, unspec_based_function, (UNSPEC_SSHLLT, UNSPEC_USHLLT, -1))
-FUNCTION (svshrnb, unspec_based_function, (UNSPEC_SHRNB, UNSPEC_SHRNB, -1))
-FUNCTION (svshrnt, unspec_based_function, (UNSPEC_SHRNT, UNSPEC_SHRNT, -1))
-FUNCTION (svsli, unspec_based_function, (UNSPEC_SLI, UNSPEC_SLI, -1))
+ UNSPEC_RSUBHNT, UNSPEC_NONE))
+FUNCTION (svsbclb, unspec_based_function, (UNSPEC_NONE, UNSPEC_SBCLB, UNSPEC_NONE))
+FUNCTION (svsbclt, unspec_based_function, (UNSPEC_NONE, UNSPEC_SBCLT, UNSPEC_NONE))
+FUNCTION (svshllb, unspec_based_function, (UNSPEC_SSHLLB, UNSPEC_USHLLB, UNSPEC_NONE))
+FUNCTION (svshllt, unspec_based_function, (UNSPEC_SSHLLT, UNSPEC_USHLLT, UNSPEC_NONE))
+FUNCTION (svshrnb, unspec_based_function, (UNSPEC_SHRNB, UNSPEC_SHRNB, UNSPEC_NONE))
+FUNCTION (svshrnt, unspec_based_function, (UNSPEC_SHRNT, UNSPEC_SHRNT, UNSPEC_NONE))
+FUNCTION (svsli, unspec_based_function, (UNSPEC_SLI, UNSPEC_SLI, UNSPEC_NONE))
FUNCTION (svsm4e, fixed_insn_function, (CODE_FOR_aarch64_sve2_sm4e))
FUNCTION (svsm4ekey, fixed_insn_function, (CODE_FOR_aarch64_sve2_sm4ekey))
FUNCTION (svsqadd, svsqadd_impl,)
FUNCTION (svsra, svsra_impl,)
-FUNCTION (svsri, unspec_based_function, (UNSPEC_SRI, UNSPEC_SRI, -1))
+FUNCTION (svsri, unspec_based_function, (UNSPEC_SRI, UNSPEC_SRI, UNSPEC_NONE))
FUNCTION (svst1dq, svst1xq_impl, (VNx1DImode))
FUNCTION (svst1q_scatter, svst1q_scatter_impl,)
FUNCTION (svst1wq, svst1xq_impl, (VNx1SImode))
FUNCTION (svstnt1b_scatter, svstnt1_scatter_truncate_impl, (QImode))
FUNCTION (svstnt1h_scatter, svstnt1_scatter_truncate_impl, (HImode))
FUNCTION (svstnt1w_scatter, svstnt1_scatter_truncate_impl, (SImode))
-FUNCTION (svsubhnb, unspec_based_function, (UNSPEC_SUBHNB, UNSPEC_SUBHNB, -1))
-FUNCTION (svsubhnt, unspec_based_function, (UNSPEC_SUBHNT, UNSPEC_SUBHNT, -1))
-FUNCTION (svsublb, unspec_based_function, (UNSPEC_SSUBLB, UNSPEC_USUBLB, -1))
-FUNCTION (svsublbt, unspec_based_function, (UNSPEC_SSUBLBT, -1, -1))
-FUNCTION (svsublt, unspec_based_function, (UNSPEC_SSUBLT, UNSPEC_USUBLT, -1))
-FUNCTION (svsubltb, unspec_based_function, (UNSPEC_SSUBLTB, -1, -1))
-FUNCTION (svsubwb, unspec_based_function, (UNSPEC_SSUBWB, UNSPEC_USUBWB, -1))
-FUNCTION (svsubwt, unspec_based_function, (UNSPEC_SSUBWT, UNSPEC_USUBWT, -1))
+FUNCTION (svsubhnb, unspec_based_function, (UNSPEC_SUBHNB, UNSPEC_SUBHNB, UNSPEC_NONE))
+FUNCTION (svsubhnt, unspec_based_function, (UNSPEC_SUBHNT, UNSPEC_SUBHNT, UNSPEC_NONE))
+FUNCTION (svsublb, unspec_based_function, (UNSPEC_SSUBLB, UNSPEC_USUBLB, UNSPEC_NONE))
+FUNCTION (svsublbt, unspec_based_function, (UNSPEC_SSUBLBT, UNSPEC_NONE, UNSPEC_NONE))
+FUNCTION (svsublt, unspec_based_function, (UNSPEC_SSUBLT, UNSPEC_USUBLT, UNSPEC_NONE))
+FUNCTION (svsubltb, unspec_based_function, (UNSPEC_SSUBLTB, UNSPEC_NONE, UNSPEC_NONE))
+FUNCTION (svsubwb, unspec_based_function, (UNSPEC_SSUBWB, UNSPEC_USUBWB, UNSPEC_NONE))
+FUNCTION (svsubwt, unspec_based_function, (UNSPEC_SSUBWT, UNSPEC_USUBWT, UNSPEC_NONE))
FUNCTION (svtbl2, svtbl2_impl,)
FUNCTION (svtblq, quiet<unspec_based_uncond_function>, (UNSPEC_TBLQ,
UNSPEC_TBLQ,
projects / thirdparty / gcc.git / commitdiff
