{"id":2226053,"url":"http://patchwork.ozlabs.org/api/patches/2226053/?format=json","web_url":"http://patchwork.ozlabs.org/project/gcc/patch/or1pg7tt1v.fsf_-_@lxoliva.fsfla.org/","project":{"id":17,"url":"http://patchwork.ozlabs.org/api/projects/17/?format=json","name":"GNU Compiler Collection","link_name":"gcc","list_id":"gcc-patches.gcc.gnu.org","list_email":"gcc-patches@gcc.gnu.org","web_url":null,"scm_url":null,"webscm_url":null,"list_archive_url":"","list_archive_url_format":"","commit_url_format":""},"msgid":"<or1pg7tt1v.fsf_-_@lxoliva.fsfla.org>","list_archive_url":null,"date":"2026-04-22T06:20:28","name":"[v2] libstdc++: simd: x86: accept 64-bit long double as double [PR124657]","commit_ref":null,"pull_url":null,"state":"new","archived":false,"hash":"1950c2cf055fa576427e03d898320fb3421318cf","submitter":{"id":74937,"url":"http://patchwork.ozlabs.org/api/people/74937/?format=json","name":"Alexandre Oliva","email":"oliva@adacore.com"},"delegate":null,"mbox":"http://patchwork.ozlabs.org/project/gcc/patch/or1pg7tt1v.fsf_-_@lxoliva.fsfla.org/mbox/","series":[{"id":500925,"url":"http://patchwork.ozlabs.org/api/series/500925/?format=json","web_url":"http://patchwork.ozlabs.org/project/gcc/list/?series=500925","date":"2026-04-22T06:20:28","name":"[v2] libstdc++: simd: x86: accept 64-bit long double as double [PR124657]","version":2,"mbox":"http://patchwork.ozlabs.org/series/500925/mbox/"}],"comments":"http://patchwork.ozlabs.org/api/patches/2226053/comments/","check":"pending","checks":"http://patchwork.ozlabs.org/api/patches/2226053/checks/","tags":{},"related":[],"headers":{"Return-Path":"<gcc-patches-bounces~incoming=patchwork.ozlabs.org@gcc.gnu.org>","X-Original-To":["incoming@patchwork.ozlabs.org","gcc-patches@gcc.gnu.org"],"Delivered-To":["patchwork-incoming@legolas.ozlabs.org","gcc-patches@gcc.gnu.org"],"Authentication-Results":["legolas.ozlabs.org;\n\tdkim=pass (2048-bit key;\n secure) header.d=adacore.com header.i=@adacore.com header.a=rsa-sha256\n header.s=google header.b=CcssgHLp;\n\tdkim-atps=neutral","legolas.ozlabs.org;\n spf=pass (sender SPF authorized) smtp.mailfrom=gcc.gnu.org\n (client-ip=2620:52:6:3111::32; helo=vm01.sourceware.org;\n envelope-from=gcc-patches-bounces~incoming=patchwork.ozlabs.org@gcc.gnu.org;\n receiver=patchwork.ozlabs.org)","sourceware.org;\n\tdkim=pass (2048-bit key,\n secure) header.d=adacore.com header.i=@adacore.com header.a=rsa-sha256\n header.s=google header.b=CcssgHLp","sourceware.org; dmarc=pass (p=quarantine dis=none)\n header.from=adacore.com","sourceware.org; spf=pass smtp.mailfrom=adacore.com","server2.sourceware.org;\n arc=none smtp.remote-ip=74.125.82.171"],"Received":["from vm01.sourceware.org (vm01.sourceware.org\n [IPv6:2620:52:6:3111::32])\n\t(using TLSv1.3 with cipher TLS_AES_256_GCM_SHA384 (256/256 bits)\n\t key-exchange x25519 server-signature ECDSA (secp384r1) server-digest SHA384)\n\t(No client certificate requested)\n\tby legolas.ozlabs.org (Postfix) with ESMTPS id 4g0pz04WH6z1y2d\n\tfor <incoming@patchwork.ozlabs.org>; Wed, 22 Apr 2026 16:21:47 +1000 (AEST)","from vm01.sourceware.org (localhost [127.0.0.1])\n\tby sourceware.org (Postfix) with ESMTP id 53F374BA9032\n\tfor <incoming@patchwork.ozlabs.org>; Wed, 22 Apr 2026 06:21:45 +0000 (GMT)","from mail-dy1-f171.google.com (mail-dy1-f171.google.com\n [74.125.82.171])\n by sourceware.org (Postfix) with ESMTPS id D78E64BA23F9\n for <gcc-patches@gcc.gnu.org>; Wed, 22 Apr 2026 06:20:46 +0000 (GMT)","by mail-dy1-f171.google.com with SMTP id\n 5a478bee46e88-2b6b0500e06so8121926eec.1\n for <gcc-patches@gcc.gnu.org>; Tue, 21 Apr 2026 23:20:46 -0700 (PDT)","from free.home ([2804:14c:4d1:41a6::2000])\n by smtp.gmail.com with ESMTPSA id\n 5a478bee46e88-2ea8e4b373dsm5341459eec.6.2026.04.21.23.20.44\n (version=TLS1_3 cipher=TLS_AES_256_GCM_SHA384 bits=256/256);\n Tue, 21 Apr 2026 23:20:44 -0700 (PDT)","from livre (livre.home [172.31.160.2])\n by free.home (8.15.2/8.15.2) with ESMTPS id 63M6KSxB032315\n (version=TLSv1.3 cipher=TLS_AES_256_GCM_SHA384 bits=256 verify=NOT);\n Wed, 22 Apr 2026 03:20:28 -0300"],"DKIM-Filter":["OpenDKIM Filter v2.11.0 sourceware.org 53F374BA9032","OpenDKIM Filter v2.11.0 sourceware.org D78E64BA23F9"],"DMARC-Filter":"OpenDMARC Filter v1.4.2 sourceware.org D78E64BA23F9","ARC-Filter":"OpenARC Filter v1.0.0 sourceware.org D78E64BA23F9","ARC-Seal":"i=1; a=rsa-sha256; d=sourceware.org; s=key; t=1776838847; cv=none;\n b=o2WOaTfH3uBBMeLu02T7qJp12UiF5KRBlJKFV76Gqs86jy9xiE6Q6kzfnTP/0OQQTnCL25O5EQ/zy3oyN5h33f+zw1VhQLwweqw4LigoVyk1MqdlbikVpxlgQATNXUgR44Fp6oPvG+i6UjQxE8nYPNl4F1LLzwFOvzk9QzPcTv8=","ARC-Message-Signature":"i=1; a=rsa-sha256; d=sourceware.org; s=key;\n t=1776838847; c=relaxed/simple;\n bh=OFAgi2DChdFpRc41L0voIB7/5X9EB1cqLMzCubCgxBw=;\n h=DKIM-Signature:From:To:Subject:Date:Message-ID:MIME-Version;\n b=MtDi5WcWnwx3X99hvEL6bqXr2maPCC9an9ghwOlJAxlHhufdyUcez4zn2QBPb+p1zbWG1v2S0rPXHqJ6R1WIFdtEcI/GjOAjmn+chuGzFLG7VdclWyKO9b6s0lUg1WyNF5cXpFqgu6AMZklGFk/jHlG5DSExySRsfKt2uRwpFw4=","ARC-Authentication-Results":"i=1; server2.sourceware.org","DKIM-Signature":"v=1; a=rsa-sha256; c=relaxed/relaxed;\n d=adacore.com; s=google; t=1776838846; x=1777443646; darn=gcc.gnu.org;\n h=mime-version:user-agent:message-id:in-reply-to:date:references\n :organization:subject:cc:to:from:from:to:cc:subject:date:message-id\n :reply-to; bh=Q446wlzZutTCDJwz8OKN+7qRzwwLNj78SH5fbqowGIE=;\n b=CcssgHLp8zoVDB1XD0u8Upo/XL6p0ks/7kf/ba8bYiQbScPBa3rg6AI7o9/1s6CNcZ\n 4ADYxkuPS2fAem1EfR5HoFPw83p05y+nvS3CVmMZZECuWlmr9jyLLr0yebfUud7rMntw\n kzK/uxccx3wpKfoRxODtqUu1WBhcO9nlhjwbXqrsTTaOslTZ2PHuiWvnFyXtYtxjcoA+\n N2MyZVgivK67+hmW2/DHAPGL+6tSbQrllv1QR7FEHtjavfs+DpkcjKp2zDosRGFEAstu\n hueu3Va5EQOWT+apWbweVO0aHdwaJ/XkiuL+luCgolHwUF6nFi+XVHPZFQFhqJqjI5JP\n Ra3Q==","X-Google-DKIM-Signature":"v=1; a=rsa-sha256; c=relaxed/relaxed;\n d=1e100.net; s=20251104; t=1776838846; x=1777443646;\n h=mime-version:user-agent:message-id:in-reply-to:date:references\n :organization:subject:cc:to:from:x-gm-gg:x-gm-message-state:from:to\n :cc:subject:date:message-id:reply-to;\n bh=Q446wlzZutTCDJwz8OKN+7qRzwwLNj78SH5fbqowGIE=;\n b=MomJHj2kx7qVTUpEadK2yQGa4mxSXxgTjTL1J8hj79PaFEt+BLhXBtbWxONvUd+OMs\n ryx0hg/uVG1Q0HCZCdvweMEs+yd3KP91w9EDl6bcbC5PDbn8a5QYcNLCy1kT7Mj7ZigC\n jnOLwqVWzNC5GNMSfMclhI79xzf6OhL3Fx2E7ZToRjkF197qG0i054ayhO39J2iE/Jfg\n s2YgmTB8UCd4xRlzGqn+tJwbc2qOsYbmgxddhq8VMcbk93egaMOsHA39OH1Xb/yj113a\n LsJppwlxLI5QlRbYdPwLjpzwZvh+1qka01IpCGC5a5yACQw7UAjSHvzAMJ7zsfGDosl6\n hY0A==","X-Forwarded-Encrypted":"i=1;\n AFNElJ8zJw0WReRvlgjjfPbcl1RRnqkdwiiw9J7SvlLiROkbJUVZGnGRmwpIzD0Ze+cx+Sn3l7qiw+MfBBg4ag==@gcc.gnu.org","X-Gm-Message-State":"AOJu0YyNT1AyaeP4sNmOlTXjcl1lJjMWx1xhTopXYTRWHKU3g34cQL3o\n iTlq1efIZ+Kp73dpAjebDIZusJJ/0uGg3aYuWgXC/8s8lJgEdiFZHKiWEhIhGUGn0g==","X-Gm-Gg":"AeBDiesJtdQtqAF6CsdXrrFYCwdFthP7vg6te0B/dlhTR24DEgcReWd0Li6ecIJ3bX1\n kIcavvDTGk8xE75s5Fv8Emj+0e+MSwR817JkJ+9h2PBh5t2X+sZjnvJz/U+1RLYtgEeerNBm4di\n EcdaPOlpo8Xuej5DVwRHwxwvpSuFpRRL570JOsIXrRCMqQLZm36Hos9FPD7RkOHCWLusi6NPJsw\n DrHp0kKIPXXW0n90fCclTQbDpiAlcBftAGOENtPoDziOY//ncM91u5PGN93sxXVzeqQsn7t6eUv\n 4lKBNdA5RfB3lt7JniC0r//1+68bwea7RC81Rb83aac6Zn8AAlcbdr0gJ8MO1CbVfbM3rbaocws\n TDkGlutwTSZ1WvozQ+UuO4+wLlnZ6Qv17P5ABRaKE6x9ZYMuTal5XlqrUr32y3ftKZ/srkHPoH2\n A6+yOa8tQs0Q==","X-Received":"by 2002:a05:693c:3007:b0:2d9:6373:ad0a with SMTP id\n 5a478bee46e88-2e46538fd04mr10451176eec.11.1776838845348;\n Tue, 21 Apr 2026 23:20:45 -0700 (PDT)","From":"Alexandre Oliva <oliva@adacore.com>","To":"Matthias Kretz <MatthiasKretz@gmx.net>","Cc":"Jonathan Wakely <jwakely@redhat.com>, libstdc++@gcc.gnu.org, Jonathan\n Wakely <jwakely.gcc@gmail.com>, gcc-patches <gcc-patches@gcc.gnu.org>","Subject":"[PATCH v2] libstdc++: simd: x86: accept 64-bit long double as\n double [PR124657]","Organization":"Free thinker, does not speak for AdaCore","References":"<oro6kdd9ji.fsf@lxoliva.fsfla.org>\n <orzf2wuczy.fsf_-_@lxoliva.fsfla.org>\n <CACb0b4nhOnWAXk7Ox05sYvHfMJMCTfYhDo9pspLjR_uW_b-BrQ@mail.gmail.com>\n <6807915.aeNJFYEL58@vir-laptop>","Date":"Wed, 22 Apr 2026 03:20:28 -0300","In-Reply-To":"<6807915.aeNJFYEL58@vir-laptop> (Matthias Kretz's message of\n \"Tue, 21 Apr 2026 10:54:48 +0200\")","Message-ID":"<or1pg7tt1v.fsf_-_@lxoliva.fsfla.org>","User-Agent":"Gnus/5.13 (Gnus v5.13) Emacs/27.1 (gnu/linux)","MIME-Version":"1.0","Content-Type":"text/plain","X-Scanned-By":"MIMEDefang 2.84","X-BeenThere":"gcc-patches@gcc.gnu.org","X-Mailman-Version":"2.1.30","Precedence":"list","List-Id":"Gcc-patches mailing list <gcc-patches.gcc.gnu.org>","List-Unsubscribe":"<https://gcc.gnu.org/mailman/options/gcc-patches>,\n <mailto:gcc-patches-request@gcc.gnu.org?subject=unsubscribe>","List-Archive":"<https://gcc.gnu.org/pipermail/gcc-patches/>","List-Post":"<mailto:gcc-patches@gcc.gnu.org>","List-Help":"<mailto:gcc-patches-request@gcc.gnu.org?subject=help>","List-Subscribe":"<https://gcc.gnu.org/mailman/listinfo/gcc-patches>,\n <mailto:gcc-patches-request@gcc.gnu.org?subject=subscribe>","Errors-To":"gcc-patches-bounces~incoming=patchwork.ozlabs.org@gcc.gnu.org"},"content":"On Apr 21, 2026, Matthias Kretz <MatthiasKretz@gmx.net> wrote:\n\n>> This would be ever so slightly more efficient as:\n\n>> because it wouldn't instantiate the is_same_v variable templates\n>> unless required, and wouldn't care about long double for the common\n>> case of 80-bit long double.\n>> \n>> But the patch seems reasonable to me. Matthias?\n\n> Yes. It looks like a clean solution to me. I like Jonathan's suggestion. \n> std::experimental::simd is too expensive to compile already.\n\nHere's a patch that implements the suggested change, and that, along\nwith https://gcc.gnu.org/pipermail/gcc-patches/2026-April/712616.html\n(Ping?) enables pr109261_constexpr_simd.cc to succeed with\n-mlong-double-64 on x86_64 -msse.  Regstrapped on x86_64-linux-gnu and\npowerpc64le-linux-gnu.  Ok for stage1?\n\nJonathan, should I credit you for the preprocessor micro-optimization?\nI didn't quite follow it to the letter, because I thought it looked\ncleaner this way, and IIUC it would not bring any notable inefficiency.\n\n\nVarious simd_x86 functions that handle double need to be adjusted to\nmatch 64-bit long double as well.\n\nIntroduce __is_x86_ps<_Tp>() and __is_x86_pd<_Tp>() and use them\ninstead of is_same_v<_Tp, float> and is_same_v<_Tp, double>,\nrespectively.\n\n\nfor  libstdc++-v3/ChangeLog\n\n\tPR libstdc++/124657\n\t* include/experimental/bits/simd_x86.h\n\t(__is_x86_ps<_Tp>): New.  Replace is_same_v<_Tp, float> with it.\n\t(__is_x86_pd<_Tp>): New.  Replace is_same_v<_Tp, double> with it.\n---\n libstdc++-v3/include/experimental/bits/simd_x86.h |   82 +++++++++++++--------\n 1 file changed, 50 insertions(+), 32 deletions(-)","diff":"diff --git a/libstdc++-v3/include/experimental/bits/simd_x86.h b/libstdc++-v3/include/experimental/bits/simd_x86.h\nindex 74c7a61998e0d..5d4ed5ad58c8e 100644\n--- a/libstdc++-v3/include/experimental/bits/simd_x86.h\n+++ b/libstdc++-v3/include/experimental/bits/simd_x86.h\n@@ -415,13 +415,31 @@ template <size_t _Np, typename _Tp, typename _Kp>\n #endif\n \n // ISA & type detection {{{\n+template <typename _Tp>\n+  constexpr bool\n+  __is_x86_ps()\n+  {\n+    return is_same_v<_Tp, float>;\n+  }\n+\n+template <typename _Tp>\n+  constexpr bool\n+  __is_x86_pd()\n+  {\n+#if __LDBL_MANT_DIG == __DBL_MANT_DIG\n+    if constexpr (is_same_v<_Tp, long double>)\n+      return true;\n+#endif\n+    return is_same_v<_Tp, double>;\n+  }\n+\n template <typename _Tp, size_t _Np>\n   constexpr bool\n   __is_sse_ps()\n   {\n     return __have_sse\n-\t   && is_same_v<_Tp,\n-\t\t\tfloat> && sizeof(__intrinsic_type_t<_Tp, _Np>) == 16;\n+\t   && __is_x86_ps<_Tp>()\n+\t   && sizeof(__intrinsic_type_t<_Tp, _Np>) == 16;\n   }\n \n template <typename _Tp, size_t _Np>\n@@ -429,8 +447,8 @@ template <typename _Tp, size_t _Np>\n   __is_sse_pd()\n   {\n     return __have_sse2\n-\t   && is_same_v<_Tp,\n-\t\t\tdouble> && sizeof(__intrinsic_type_t<_Tp, _Np>) == 16;\n+\t   && __is_x86_pd<_Tp>()\n+\t   && sizeof(__intrinsic_type_t<_Tp, _Np>) == 16;\n   }\n \n template <typename _Tp, size_t _Np>\n@@ -438,8 +456,8 @@ template <typename _Tp, size_t _Np>\n   __is_avx_ps()\n   {\n     return __have_avx\n-\t   && is_same_v<_Tp,\n-\t\t\tfloat> && sizeof(__intrinsic_type_t<_Tp, _Np>) == 32;\n+\t   && __is_x86_ps<_Tp>()\n+\t   && sizeof(__intrinsic_type_t<_Tp, _Np>) == 32;\n   }\n \n template <typename _Tp, size_t _Np>\n@@ -447,8 +465,8 @@ template <typename _Tp, size_t _Np>\n   __is_avx_pd()\n   {\n     return __have_avx\n-\t   && is_same_v<_Tp,\n-\t\t\tdouble> && sizeof(__intrinsic_type_t<_Tp, _Np>) == 32;\n+\t   && __is_x86_pd<_Tp>()\n+\t   && sizeof(__intrinsic_type_t<_Tp, _Np>) == 32;\n   }\n \n template <typename _Tp, size_t _Np>\n@@ -456,8 +474,8 @@ template <typename _Tp, size_t _Np>\n   __is_avx512_ps()\n   {\n     return __have_avx512f\n-\t   && is_same_v<_Tp,\n-\t\t\tfloat> && sizeof(__intrinsic_type_t<_Tp, _Np>) == 64;\n+\t   && __is_x86_ps<_Tp>()\n+\t   && sizeof(__intrinsic_type_t<_Tp, _Np>) == 64;\n   }\n \n template <typename _Tp, size_t _Np>\n@@ -465,8 +483,8 @@ template <typename _Tp, size_t _Np>\n   __is_avx512_pd()\n   {\n     return __have_avx512f\n-\t   && is_same_v<_Tp,\n-\t\t\tdouble> && sizeof(__intrinsic_type_t<_Tp, _Np>) == 64;\n+\t   && __is_x86_pd<_Tp>()\n+\t   && sizeof(__intrinsic_type_t<_Tp, _Np>) == 64;\n   }\n \n // }}}\n@@ -2397,9 +2415,9 @@ template <typename _Abi, typename>\n \t    [[maybe_unused]] const auto __yi = __to_intrin(__y);\n \t    if constexpr (sizeof(__xi) == 64)\n \t      {\n-\t\tif constexpr (is_same_v<_Tp, float>)\n+\t\tif constexpr (__is_x86_ps<_Tp> ())\n \t\t  return _mm512_mask_cmp_ps_mask(__k1, __xi, __yi, _CMP_LT_OS);\n-\t\telse if constexpr (is_same_v<_Tp, double>)\n+\t\telse if constexpr (__is_x86_pd<_Tp> ())\n \t\t  return _mm512_mask_cmp_pd_mask(__k1, __xi, __yi, _CMP_LT_OS);\n \t\telse if constexpr (is_signed_v<_Tp> && sizeof(_Tp) == 1)\n \t\t  return _mm512_mask_cmplt_epi8_mask(__k1, __xi, __yi);\n@@ -2422,9 +2440,9 @@ template <typename _Abi, typename>\n \t      }\n \t    else if constexpr (sizeof(__xi) == 32)\n \t      {\n-\t\tif constexpr (is_same_v<_Tp, float>)\n+\t\tif constexpr (__is_x86_ps<_Tp> ())\n \t\t  return _mm256_mask_cmp_ps_mask(__k1, __xi, __yi, _CMP_LT_OS);\n-\t\telse if constexpr (is_same_v<_Tp, double>)\n+\t\telse if constexpr (__is_x86_pd<_Tp> ())\n \t\t  return _mm256_mask_cmp_pd_mask(__k1, __xi, __yi, _CMP_LT_OS);\n \t\telse if constexpr (is_signed_v<_Tp> && sizeof(_Tp) == 1)\n \t\t  return _mm256_mask_cmplt_epi8_mask(__k1, __xi, __yi);\n@@ -2447,9 +2465,9 @@ template <typename _Abi, typename>\n \t      }\n \t    else if constexpr (sizeof(__xi) == 16)\n \t      {\n-\t\tif constexpr (is_same_v<_Tp, float>)\n+\t\tif constexpr (__is_x86_ps<_Tp> ())\n \t\t  return _mm_mask_cmp_ps_mask(__k1, __xi, __yi, _CMP_LT_OS);\n-\t\telse if constexpr (is_same_v<_Tp, double>)\n+\t\telse if constexpr (__is_x86_pd<_Tp> ())\n \t\t  return _mm_mask_cmp_pd_mask(__k1, __xi, __yi, _CMP_LT_OS);\n \t\telse if constexpr (is_signed_v<_Tp> && sizeof(_Tp) == 1)\n \t\t  return _mm_mask_cmplt_epi8_mask(__k1, __xi, __yi);\n@@ -2505,9 +2523,9 @@ template <typename _Abi, typename>\n \t    [[maybe_unused]] const auto __yi = __to_intrin(__y);\n \t    if constexpr (sizeof(__xi) == 64)\n \t      {\n-\t\tif constexpr (is_same_v<_Tp, float>)\n+\t\tif constexpr (__is_x86_ps<_Tp> ())\n \t\t  return _mm512_mask_cmp_ps_mask(__k1, __xi, __yi, _CMP_LE_OS);\n-\t\telse if constexpr (is_same_v<_Tp, double>)\n+\t\telse if constexpr (__is_x86_pd<_Tp> ())\n \t\t  return _mm512_mask_cmp_pd_mask(__k1, __xi, __yi, _CMP_LE_OS);\n \t\telse if constexpr (is_signed_v<_Tp> && sizeof(_Tp) == 1)\n \t\t  return _mm512_mask_cmple_epi8_mask(__k1, __xi, __yi);\n@@ -2530,9 +2548,9 @@ template <typename _Abi, typename>\n \t      }\n \t    else if constexpr (sizeof(__xi) == 32)\n \t      {\n-\t\tif constexpr (is_same_v<_Tp, float>)\n+\t\tif constexpr (__is_x86_ps<_Tp> ())\n \t\t  return _mm256_mask_cmp_ps_mask(__k1, __xi, __yi, _CMP_LE_OS);\n-\t\telse if constexpr (is_same_v<_Tp, double>)\n+\t\telse if constexpr (__is_x86_pd<_Tp> ())\n \t\t  return _mm256_mask_cmp_pd_mask(__k1, __xi, __yi, _CMP_LE_OS);\n \t\telse if constexpr (is_signed_v<_Tp> && sizeof(_Tp) == 1)\n \t\t  return _mm256_mask_cmple_epi8_mask(__k1, __xi, __yi);\n@@ -2555,9 +2573,9 @@ template <typename _Abi, typename>\n \t      }\n \t    else if constexpr (sizeof(__xi) == 16)\n \t      {\n-\t\tif constexpr (is_same_v<_Tp, float>)\n+\t\tif constexpr (__is_x86_ps<_Tp> ())\n \t\t  return _mm_mask_cmp_ps_mask(__k1, __xi, __yi, _CMP_LE_OS);\n-\t\telse if constexpr (is_same_v<_Tp, double>)\n+\t\telse if constexpr (__is_x86_pd<_Tp> ())\n \t\t  return _mm_mask_cmp_pd_mask(__k1, __xi, __yi, _CMP_LE_OS);\n \t\telse if constexpr (is_signed_v<_Tp> && sizeof(_Tp) == 1)\n \t\t  return _mm_mask_cmple_epi8_mask(__k1, __xi, __yi);\n@@ -5021,10 +5039,10 @@ template <typename _Abi, typename>\n \t\t  = _Abi::template _S_implicit_mask_intrin<_Tp>();\n \t\treturn 0 != __testc(__a, __b);\n \t      }\n-\t    else if constexpr (is_same_v<_Tp, float>)\n+\t    else if constexpr (__is_x86_ps<_Tp> ())\n \t      return (_mm_movemask_ps(__a) & ((1 << _Np) - 1))\n \t\t     == (1 << _Np) - 1;\n-\t    else if constexpr (is_same_v<_Tp, double>)\n+\t    else if constexpr (__is_x86_pd<_Tp> ())\n \t      return (_mm_movemask_pd(__a) & ((1 << _Np) - 1))\n \t\t     == (1 << _Np) - 1;\n \t    else\n@@ -5084,9 +5102,9 @@ template <typename _Abi, typename>\n \t\telse\n \t\t  return 0 == __testz(__a, __a);\n \t      }\n-\t    else if constexpr (is_same_v<_Tp, float>)\n+\t    else if constexpr (__is_x86_ps<_Tp> ())\n \t      return (_mm_movemask_ps(__a) & ((1 << _Np) - 1)) != 0;\n-\t    else if constexpr (is_same_v<_Tp, double>)\n+\t    else if constexpr (__is_x86_pd<_Tp> ())\n \t      return (_mm_movemask_pd(__a) & ((1 << _Np) - 1)) != 0;\n \t    else\n \t      return (_mm_movemask_epi8(__a) & ((1 << (_Np * sizeof(_Tp))) - 1))\n@@ -5120,9 +5138,9 @@ template <typename _Abi, typename>\n \t\telse\n \t\t  return 0 != __testz(__a, __a);\n \t      }\n-\t    else if constexpr (is_same_v<_Tp, float>)\n+\t    else if constexpr (__is_x86_ps<_Tp> ())\n \t      return (__movemask(__a) & ((1 << _Np) - 1)) == 0;\n-\t    else if constexpr (is_same_v<_Tp, double>)\n+\t    else if constexpr (__is_x86_pd<_Tp> ())\n \t      return (__movemask(__a) & ((1 << _Np) - 1)) == 0;\n \t    else\n \t      return (__movemask(__a) & int((1ull << (_Np * sizeof(_Tp))) - 1))\n@@ -5150,13 +5168,13 @@ template <typename _Abi, typename>\n \t\t  = _Abi::template _S_implicit_mask_intrin<_Tp>();\n \t\treturn 0 != __testnzc(__a, __b);\n \t      }\n-\t    else if constexpr (is_same_v<_Tp, float>)\n+\t    else if constexpr (__is_x86_ps<_Tp> ())\n \t      {\n \t\tconstexpr int __allbits = (1 << _Np) - 1;\n \t\tconst auto __tmp = _mm_movemask_ps(__a) & __allbits;\n \t\treturn __tmp > 0 && __tmp < __allbits;\n \t      }\n-\t    else if constexpr (is_same_v<_Tp, double>)\n+\t    else if constexpr (__is_x86_pd<_Tp> ())\n \t      {\n \t\tconstexpr int __allbits = (1 << _Np) - 1;\n \t\tconst auto __tmp = _mm_movemask_pd(__a) & __allbits;\n","prefixes":["v2"]}