From patchwork Wed Nov 29 03:16:59 2023 Content-Type: text/plain; charset="utf-8" MIME-Version: 1.0 Content-Transfer-Encoding: 7bit X-Patchwork-Submitter: Jiahao Xu X-Patchwork-Id: 171044 Return-Path: Delivered-To: ouuuleilei@gmail.com Received: by 2002:a59:a5a7:0:b0:403:3b70:6f57 with SMTP id d7csp92275vqn; Tue, 28 Nov 2023 19:17:52 -0800 (PST) X-Google-Smtp-Source: AGHT+IHyIJfrXDevLZpUa9knDaOGhwvpwckwFAx6aKIM1RGmPPyK9wYBdfSyp5NtjlnjAVn0uerU X-Received: by 2002:a05:622a:10c:b0:423:6f05:33da with SMTP id u12-20020a05622a010c00b004236f0533damr21340461qtw.18.1701227872269; Tue, 28 Nov 2023 19:17:52 -0800 (PST) ARC-Seal: i=2; a=rsa-sha256; t=1701227872; cv=pass; d=google.com; s=arc-20160816; b=a+0EFvki8/w4Y9vWrvuPZKO6V6LaoWzR46THDhIWiWsFfkwfLPRQHlMg5lq6LMSkh5 rFEzVZJI1s4pIdKkD632WLkj+tPjaPCRnOQgkJhXPvFHsYN6fnewQTRnU285kWOrQ5ek h1bNqdPyLhPkAgTZFRu5/N1PupihWMDUQUIeLnGjRkxHOVy4ZBUTeygCETDWhVNTIrkO J+zMD1v4nWLd182PlFCqUYTF+dNXxmkrpmQhXesjhKgdgTxxC4uFnnDlEUJB0h2uVxfX FCA2sWI1C6t1ESyr77Jk8O7Goe6l+ZKvoBSAVq9Lyv0w7n1FCO1lf2h4jXXOPZiq8OFg +W6w== ARC-Message-Signature: i=2; a=rsa-sha256; c=relaxed/relaxed; d=google.com; s=arc-20160816; h=errors-to:list-subscribe:list-help:list-post:list-archive :list-unsubscribe:list-id:precedence:content-transfer-encoding :mime-version:message-id:date:subject:cc:to:from:arc-filter :dmarc-filter:delivered-to; bh=qhkMntIGlOOLM/L/GhnDzdvrOVA3ze5udqm2HByBvJY=; fh=w+xsGLuzpTj56E0bzPMCc39RWHkBXt2f2AGs+4pGimo=; b=XTbEQyltSAms7QwM/E1+Su7oSaXzrMgBaRLUJgVw/vBmOGpJBLwC15/eYZH3HYRMhL URu8DE/bPObtLDdKkkX/LThctUiEeRqTeMbB/Me/fBzq8LBDV3iZtKl02WeNLYTHSss9 5iqWd62TSI3eC7L3sj24hxDAQqgNTHkFOjOrcTR3K1kclXW8ZL8xYbHDhtE1qSP391E5 sLzD/qeGd0Lwy6It4L67wfPyzPyw2ZaayteYAXy0ptidvTBJhxFpqmqqEcrbg04hOrNe Z0AgyOWdHgbMO+2Aa1GxSIDSSBzZ5F68/0Ar89mh7wrUTXZtXarD8l3a9aaxmpnVI2vN lE9A== ARC-Authentication-Results: i=2; mx.google.com; arc=pass (i=1); spf=pass (google.com: domain of gcc-patches-bounces+ouuuleilei=gmail.com@gcc.gnu.org designates 2620:52:3:1:0:246e:9693:128c as permitted sender) smtp.mailfrom="gcc-patches-bounces+ouuuleilei=gmail.com@gcc.gnu.org" Received: from server2.sourceware.org (server2.sourceware.org. [2620:52:3:1:0:246e:9693:128c]) by mx.google.com with ESMTPS id o1-20020ac85a41000000b0041230bc1d65si12931918qta.371.2023.11.28.19.17.52 for (version=TLS1_3 cipher=TLS_AES_256_GCM_SHA384 bits=256/256); Tue, 28 Nov 2023 19:17:52 -0800 (PST) Received-SPF: pass (google.com: domain of gcc-patches-bounces+ouuuleilei=gmail.com@gcc.gnu.org designates 2620:52:3:1:0:246e:9693:128c as permitted sender) client-ip=2620:52:3:1:0:246e:9693:128c; Authentication-Results: mx.google.com; arc=pass (i=1); spf=pass (google.com: domain of gcc-patches-bounces+ouuuleilei=gmail.com@gcc.gnu.org designates 2620:52:3:1:0:246e:9693:128c as permitted sender) smtp.mailfrom="gcc-patches-bounces+ouuuleilei=gmail.com@gcc.gnu.org" Received: from server2.sourceware.org (localhost [IPv6:::1]) by sourceware.org (Postfix) with ESMTP id 0B407385701C for ; Wed, 29 Nov 2023 03:17:52 +0000 (GMT) X-Original-To: gcc-patches@gcc.gnu.org Delivered-To: gcc-patches@gcc.gnu.org Received: from eggs.gnu.org (eggs.gnu.org [IPv6:2001:470:142:3::10]) by sourceware.org (Postfix) with ESMTPS id E80CA3858D3C for ; Wed, 29 Nov 2023 03:17:23 +0000 (GMT) DMARC-Filter: OpenDMARC Filter v1.4.2 sourceware.org E80CA3858D3C Authentication-Results: sourceware.org; dmarc=none (p=none dis=none) header.from=loongson.cn Authentication-Results: sourceware.org; spf=fail smtp.mailfrom=loongson.cn ARC-Filter: OpenARC Filter v1.0.0 sourceware.org E80CA3858D3C Authentication-Results: server2.sourceware.org; arc=none smtp.remote-ip=2001:470:142:3::10 ARC-Seal: i=1; a=rsa-sha256; d=sourceware.org; s=key; t=1701227848; cv=none; b=CQja4xSaA7YFhuy3XwgYccZ5c7vpnFjVNCH3axIX+SszPPbttmawulMxzOilXisNGeQehij3nHhJIehy4DmgcjSx/FkBnP3ENTuIvG1ZZXNWzttdAMFaOJIg5spWpF7wLGQQWaWGkjNq89UXtQl24E1FV2EC1p8v2JVQyQFEWPQ= ARC-Message-Signature: i=1; a=rsa-sha256; d=sourceware.org; s=key; t=1701227848; c=relaxed/simple; bh=5WfQ7c//cu3Uw+JtL4Z3Azm+8EWCN6KeoI81uGXyw/o=; h=From:To:Subject:Date:Message-Id:MIME-Version; b=UdNCsgHKmfAhCIsEnwArtk7mCaJwce15LnomPkfIj6p1jNwfISHxMzz45lqylEg3i//C9tirukaqyIb7/dNveA59TzJ33GFJdY1VVnNg13Zt7ezjTR80lYiPIlmKidCyqUKlC5rfHvhZR2aapfcM65hnwpSiTDpc+2w0LYf7WVk= ARC-Authentication-Results: i=1; server2.sourceware.org Received: from mail.loongson.cn ([114.242.206.163]) by eggs.gnu.org with esmtp (Exim 4.90_1) (envelope-from ) id 1r8B4f-00034L-Iw for gcc-patches@gcc.gnu.org; Tue, 28 Nov 2023 22:17:23 -0500 Received: from loongson.cn (unknown [10.10.130.252]) by gateway (Coremail) with SMTP id _____8CxRugvrWZl2pE9AA--.3162S3; Wed, 29 Nov 2023 11:17:04 +0800 (CST) Received: from slurm-master.loongson.cn (unknown [10.10.130.252]) by localhost.localdomain (Coremail) with SMTP id AQAAf8CxvdwurWZlEGlPAA--.45090S4; Wed, 29 Nov 2023 11:17:02 +0800 (CST) From: Jiahao Xu To: gcc-patches@gcc.gnu.org Cc: xry111@xry111.site, i@xen0n.name, chenglulu@loongson.cn, xuchenghua@loongson.cn, Jiahao Xu Subject: [PATCH] LoongArch: Fix lsx-vshuf.c and lasx-xvshuf_b.c tests fail on LA664 [PR112611] Date: Wed, 29 Nov 2023 11:16:59 +0800 Message-Id: <20231129031659.17376-1-xujiahao@loongson.cn> X-Mailer: git-send-email 2.20.1 MIME-Version: 1.0 X-CM-TRANSID: AQAAf8CxvdwurWZlEGlPAA--.45090S4 X-CM-SenderInfo: 50xmxthkdrqz5rrqw2lrqou0/ X-Coremail-Antispam: 1Uk129KBj9UXoWxGF48Kr15trW5KoXrpF17uF1Upr17tr1fKr WI9a4UKryDJFyaqrWUJr4vyasrJF17t3sF93WkKFn0qr13C3yDJw4DAFyDZF13tFy5Jr4j qr45JwcCm3ZEXasCq-sJn29KB7ZKAUJUUUU5529EdanIXcx71UUUUU7KY7ZEXasCq-sGcS sGvfJ3Ic02F40EFcxC0VAKzVAqx4xG6I80ebIjqfuFe4nvWSU5nxnvy29KBjDU0xBIdaVr nRJUUUkYb4IE77IF4wAFF20E14v26r1j6r4UM7CY07I20VC2zVCF04k26cxKx2IYs7xG6r Wj6s0DM7CIcVAFz4kK6r1j6r18M28lY4IEw2IIxxk0rwA2F7IY1VAKz4vEj48ve4kI8wA2 z4x0Y4vE2Ix0cI8IcVAFwI0_JFI_Gr1l84ACjcxK6xIIjxv20xvEc7CjxVAFwI0_Gr0_Cr 1l84ACjcxK6I8E87Iv67AKxVWxJVW8Jr1l84ACjcxK6I8E87Iv6xkF7I0E14v26r4UJVWx Jr1le2I262IYc4CY6c8Ij28IcVAaY2xG8wAqjxCEc2xF0cIa020Ex4CE44I27wAqx4xG64 xvF2IEw4CE5I8CrVC2j2WlYx0E2Ix0cI8IcVAFwI0_Jrv_JF1lYx0Ex4A2jsIE14v26r1j 6r4UMcvjeVCFs4IE7xkEbVWUJVW8JwACjcxG0xvY0x0EwIxGrwCF04k20xvY0x0EwIxGrw CFx2IqxVCFs4IE7xkEbVWUJVW8JwC20s026c02F40E14v26r1j6r18MI8I3I0E7480Y4vE 14v26r106r1rMI8E67AF67kF1VAFwI0_JF0_Jw1lIxkGc2Ij64vIr41lIxAIcVC0I7IYx2 IY67AKxVWUJVWUCwCI42IY6xIIjxv20xvEc7CjxVAFwI0_Jr0_Gr1lIxAIcVCF04k26cxK x2IYs7xG6r1j6r1xMIIF0xvEx4A2jsIE14v26r1j6r4UMIIF0xvEx4A2jsIEc7CjxVAFwI 0_Jr0_GrUvcSsGvfC2KfnxnUUI43ZEXa7IU1QVy3UUUUU== Received-SPF: pass client-ip=114.242.206.163; envelope-from=xujiahao@loongson.cn; helo=mail.loongson.cn X-Spam_score_int: -18 X-Spam_score: -1.9 X-Spam_bar: - X-Spam_report: (-1.9 / 5.0 requ) BAYES_00=-1.9, SPF_HELO_NONE=0.001, SPF_PASS=-0.001, T_SCC_BODY_TEXT_LINE=-0.01 autolearn=ham autolearn_force=no X-Spam_action: no action X-Spam-Status: No, score=-13.5 required=5.0 tests=BAYES_00, GIT_PATCH_0, KAM_DMARC_STATUS, KAM_SHORT, SPF_FAIL, SPF_HELO_PASS, TXREP, T_SCC_BODY_TEXT_LINE autolearn=ham autolearn_force=no version=3.4.6 X-Spam-Checker-Version: SpamAssassin 3.4.6 (2021-04-09) on server2.sourceware.org X-BeenThere: gcc-patches@gcc.gnu.org X-Mailman-Version: 2.1.30 Precedence: list List-Id: Gcc-patches mailing list List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , Errors-To: gcc-patches-bounces+ouuuleilei=gmail.com@gcc.gnu.org X-getmail-retrieved-from-mailbox: INBOX X-GMAIL-THRID: 1783866717060895793 X-GMAIL-MSGID: 1783866717060895793 For [x]vshuf instructions, if the index value in the selector exceeds 63, it triggers undefined behavior on LA464, but not on LA664. To ensure compatibility of these two tests on both LA464 and LA664, we have modified both tests to ensure that the index value in the selector does not exceed 63. gcc/testsuite/ChangeLog: * gcc.target/loongarch/vector/lasx/lasx-xvshuf_b.c: Sure index less than 64. * gcc.target/loongarch/vector/lsx/lsx-vshuf.c: Ditto. diff --git a/gcc/testsuite/gcc.target/loongarch/vector/lasx/lasx-xvshuf_b.c b/gcc/testsuite/gcc.target/loongarch/vector/lasx/lasx-xvshuf_b.c index 641ea2315ff..03c479a085c 100644 --- a/gcc/testsuite/gcc.target/loongarch/vector/lasx/lasx-xvshuf_b.c +++ b/gcc/testsuite/gcc.target/loongarch/vector/lasx/lasx-xvshuf_b.c @@ -44,9 +44,9 @@ main () *((unsigned long *)&__m256i_op1[1]) = 0xfffffefefffffefe; *((unsigned long *)&__m256i_op1[0]) = 0xfffffefefffffefe; *((unsigned long *)&__m256i_op2[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op2[2]) = 0xfffffff8fffffff8; + *((unsigned long *)&__m256i_op2[2]) = 0x3f3f3f383f3f3f38; *((unsigned long *)&__m256i_op2[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op2[0]) = 0xfffffff8fc000000; + *((unsigned long *)&__m256i_op2[0]) = 0x3f3f3f383c000000; *((unsigned long *)&__m256i_result[3]) = 0xfafafafafafafafa; *((unsigned long *)&__m256i_result[2]) = 0x0000000000000000; *((unsigned long *)&__m256i_result[1]) = 0xfefefefefefefefe; @@ -138,33 +138,14 @@ main () *((unsigned long *)&__m256i_op1[2]) = 0xffffffffffffffff; *((unsigned long *)&__m256i_op1[1]) = 0x0000000000000000; *((unsigned long *)&__m256i_op1[0]) = 0xffffffffffffffff; - *((unsigned long *)&__m256i_op2[3]) = 0x0000ffffffffffff; - *((unsigned long *)&__m256i_op2[2]) = 0x0000ffff0000ffff; - *((unsigned long *)&__m256i_op2[1]) = 0x0000ffffffffffff; - *((unsigned long *)&__m256i_op2[0]) = 0x0000ffff0000ffff; + *((unsigned long *)&__m256i_op2[3]) = 0x0000111111111111; + *((unsigned long *)&__m256i_op2[2]) = 0x0000222200002222; + *((unsigned long *)&__m256i_op2[1]) = 0x0000111111111111; + *((unsigned long *)&__m256i_op2[0]) = 0x0000222200002222; *((unsigned long *)&__m256i_result[3]) = 0xffff000000000000; - *((unsigned long *)&__m256i_result[2]) = 0xffff0000ffff0000; + *((unsigned long *)&__m256i_result[2]) = 0xffffffffffffffff; *((unsigned long *)&__m256i_result[1]) = 0xffff000000000000; - *((unsigned long *)&__m256i_result[0]) = 0xffff0000ffff0000; - __m256i_out = __lasx_xvshuf_b (__m256i_op0, __m256i_op1, __m256i_op2); - ASSERTEQ_64 (__LINE__, __m256i_result, __m256i_out); - - *((unsigned long *)&__m256i_op0[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op0[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op0[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op0[0]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op1[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op1[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op1[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op1[0]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op2[3]) = 0x000000000000ffff; - *((unsigned long *)&__m256i_op2[2]) = 0x000000000000ffff; - *((unsigned long *)&__m256i_op2[1]) = 0x000000000000ffff; - *((unsigned long *)&__m256i_op2[0]) = 0x000000000000ffff; - *((unsigned long *)&__m256i_result[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[0]) = 0x0000000000000000; + *((unsigned long *)&__m256i_result[0]) = 0xffffffffffffffff; __m256i_out = __lasx_xvshuf_b (__m256i_op0, __m256i_op1, __m256i_op2); ASSERTEQ_64 (__LINE__, __m256i_result, __m256i_out); @@ -177,7 +158,7 @@ main () *((unsigned long *)&__m256i_op1[1]) = 0x0000000000000000; *((unsigned long *)&__m256i_op1[0]) = 0x0000000000000000; *((unsigned long *)&__m256i_op2[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op2[2]) = 0x0000000000077fff; + *((unsigned long *)&__m256i_op2[2]) = 0x0000000000032f1f; *((unsigned long *)&__m256i_op2[1]) = 0x0000000000000000; *((unsigned long *)&__m256i_op2[0]) = 0x0000000000000000; *((unsigned long *)&__m256i_result[3]) = 0xffffffffffffffff; @@ -187,9 +168,9 @@ main () __m256i_out = __lasx_xvshuf_b (__m256i_op0, __m256i_op1, __m256i_op2); ASSERTEQ_64 (__LINE__, __m256i_result, __m256i_out); - *((unsigned long *)&__m256i_op0[3]) = 0xfffffffffffffefe; - *((unsigned long *)&__m256i_op0[2]) = 0x0000000000000101; - *((unsigned long *)&__m256i_op0[1]) = 0xfffffffffffffefe; + *((unsigned long *)&__m256i_op0[3]) = 0x0011001100110011; + *((unsigned long *)&__m256i_op0[2]) = 0x0000000000000001; + *((unsigned long *)&__m256i_op0[1]) = 0x0011001100110011; *((unsigned long *)&__m256i_op0[0]) = 0x0000000000000101; *((unsigned long *)&__m256i_op1[3]) = 0xffffffffffffffff; *((unsigned long *)&__m256i_op1[2]) = 0x67eee33567eee435; @@ -199,35 +180,16 @@ main () *((unsigned long *)&__m256i_op2[2]) = 0xffffffffffffffff; *((unsigned long *)&__m256i_op2[1]) = 0x00000000ffffffff; *((unsigned long *)&__m256i_op2[0]) = 0xffffffffffffffff; - *((unsigned long *)&__m256i_result[3]) = 0x0000000000000000; + *((unsigned long *)&__m256i_result[3]) = 0xffffffffffffffff; *((unsigned long *)&__m256i_result[2]) = 0xffffffffffffffff; - *((unsigned long *)&__m256i_result[1]) = 0x0000000000000000; + *((unsigned long *)&__m256i_result[1]) = 0xffffffffffffffff; *((unsigned long *)&__m256i_result[0]) = 0xffffffffffffffff; __m256i_out = __lasx_xvshuf_h (__m256i_op0, __m256i_op1, __m256i_op2); ASSERTEQ_64 (__LINE__, __m256i_result, __m256i_out); - *((unsigned long *)&__m256i_op0[3]) = 0x0000000000000000; + *((unsigned long *)&__m256i_op0[3]) = 0x0022002200000000; *((unsigned long *)&__m256i_op0[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op0[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op0[0]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op1[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op1[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op1[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op1[0]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op2[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op2[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op2[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op2[0]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[0]) = 0x0000000000000000; - __m256i_out = __lasx_xvshuf_h (__m256i_op0, __m256i_op1, __m256i_op2); - ASSERTEQ_64 (__LINE__, __m256i_result, __m256i_out); - - *((unsigned long *)&__m256i_op0[3]) = 0xffffffff80000000; - *((unsigned long *)&__m256i_op0[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op0[1]) = 0xffffffff80000000; + *((unsigned long *)&__m256i_op0[1]) = 0x001f001f00000000; *((unsigned long *)&__m256i_op0[0]) = 0x0000000000000000; *((unsigned long *)&__m256i_op1[3]) = 0xffffffffffffffff; *((unsigned long *)&__m256i_op1[2]) = 0xffffffffffffffff; @@ -244,10 +206,10 @@ main () __m256i_out = __lasx_xvshuf_h (__m256i_op0, __m256i_op1, __m256i_op2); ASSERTEQ_64 (__LINE__, __m256i_result, __m256i_out); - *((unsigned long *)&__m256i_op0[3]) = 0xffffffffffffffff; - *((unsigned long *)&__m256i_op0[2]) = 0xffffffffffffffff; - *((unsigned long *)&__m256i_op0[1]) = 0xffffffffffffffff; - *((unsigned long *)&__m256i_op0[0]) = 0xffffffffffffffff; + *((unsigned long *)&__m256i_op0[3]) = 0x0011001100110011; + *((unsigned long *)&__m256i_op0[2]) = 0x0011001100110011; + *((unsigned long *)&__m256i_op0[1]) = 0x0011001100110011; + *((unsigned long *)&__m256i_op0[0]) = 0x0011001100110011; *((unsigned long *)&__m256i_op1[3]) = 0xffffffffffffffff; *((unsigned long *)&__m256i_op1[2]) = 0xffffffffffffffff; *((unsigned long *)&__m256i_op1[1]) = 0xffffffffffffffff; @@ -256,17 +218,17 @@ main () *((unsigned long *)&__m256i_op2[2]) = 0xffffffffffffffff; *((unsigned long *)&__m256i_op2[1]) = 0xffffffffffffffff; *((unsigned long *)&__m256i_op2[0]) = 0xffffffffffffffff; - *((unsigned long *)&__m256i_result[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[0]) = 0x0000000000000000; + *((unsigned long *)&__m256i_result[3]) = 0xffffffffffffffff; + *((unsigned long *)&__m256i_result[2]) = 0xffffffffffffffff; + *((unsigned long *)&__m256i_result[1]) = 0xffffffffffffffff; + *((unsigned long *)&__m256i_result[0]) = 0xffffffffffffffff; __m256i_out = __lasx_xvshuf_h (__m256i_op0, __m256i_op1, __m256i_op2); ASSERTEQ_64 (__LINE__, __m256i_result, __m256i_out); - *((unsigned long *)&__m256i_op0[3]) = 0xffffffffffffffff; - *((unsigned long *)&__m256i_op0[2]) = 0xffffffffffffffff; - *((unsigned long *)&__m256i_op0[1]) = 0xffffffffffffffff; - *((unsigned long *)&__m256i_op0[0]) = 0xffffffffffffffff; + *((unsigned long *)&__m256i_op0[3]) = 0x003f003f003f003f; + *((unsigned long *)&__m256i_op0[2]) = 0x003f003f003f003f; + *((unsigned long *)&__m256i_op0[1]) = 0x003f003f003f003f; + *((unsigned long *)&__m256i_op0[0]) = 0x003f003f003f003f; *((unsigned long *)&__m256i_op1[3]) = 0xefdfefdf00000000; *((unsigned long *)&__m256i_op1[2]) = 0xefdfefdfefdfefdf; *((unsigned long *)&__m256i_op1[1]) = 0xefdfefdf00000000; @@ -275,36 +237,17 @@ main () *((unsigned long *)&__m256i_op2[2]) = 0xffffffffffffffff; *((unsigned long *)&__m256i_op2[1]) = 0xffffffffffffffff; *((unsigned long *)&__m256i_op2[0]) = 0xffffffffffffffff; - *((unsigned long *)&__m256i_result[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[0]) = 0x0000000000000000; - __m256i_out = __lasx_xvshuf_h (__m256i_op0, __m256i_op1, __m256i_op2); - ASSERTEQ_64 (__LINE__, __m256i_result, __m256i_out); - - *((unsigned long *)&__m256i_op0[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op0[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op0[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op0[0]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op1[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op1[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op1[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op1[0]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op2[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op2[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op2[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op2[0]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[0]) = 0x0000000000000000; + *((unsigned long *)&__m256i_result[3]) = 0xefdfefdfefdfefdf; + *((unsigned long *)&__m256i_result[2]) = 0xefdfefdfefdfefdf; + *((unsigned long *)&__m256i_result[1]) = 0xefdfefdfefdfefdf; + *((unsigned long *)&__m256i_result[0]) = 0xefdfefdfefdfefdf; __m256i_out = __lasx_xvshuf_h (__m256i_op0, __m256i_op1, __m256i_op2); ASSERTEQ_64 (__LINE__, __m256i_result, __m256i_out); - *((unsigned long *)&__m256i_op0[3]) = 0x7575ffff75757595; - *((unsigned long *)&__m256i_op0[2]) = 0x7575ffff7575f575; - *((unsigned long *)&__m256i_op0[1]) = 0x7575ffff75757595; - *((unsigned long *)&__m256i_op0[0]) = 0x7575ffff7575f575; + *((unsigned long *)&__m256i_op0[3]) = 0x0035000000350005; + *((unsigned long *)&__m256i_op0[2]) = 0x0035000000350015; + *((unsigned long *)&__m256i_op0[1]) = 0x0035000000350025; + *((unsigned long *)&__m256i_op0[0]) = 0x0035000000350035; *((unsigned long *)&__m256i_op1[3]) = 0x0000000000000003; *((unsigned long *)&__m256i_op1[2]) = 0x0000000000010001; *((unsigned long *)&__m256i_op1[1]) = 0x0000000000000003; @@ -313,10 +256,10 @@ main () *((unsigned long *)&__m256i_op2[2]) = 0x7575757575757575; *((unsigned long *)&__m256i_op2[1]) = 0x7575757575757575; *((unsigned long *)&__m256i_op2[0]) = 0x7575757575757575; - *((unsigned long *)&__m256i_result[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[0]) = 0x0000000000000000; + *((unsigned long *)&__m256i_result[3]) = 0x7575757575757575; + *((unsigned long *)&__m256i_result[2]) = 0x7575757575757575; + *((unsigned long *)&__m256i_result[1]) = 0x7575757575757575; + *((unsigned long *)&__m256i_result[0]) = 0x7575757575757575; __m256i_out = __lasx_xvshuf_h (__m256i_op0, __m256i_op1, __m256i_op2); ASSERTEQ_64 (__LINE__, __m256i_result, __m256i_out); @@ -358,29 +301,10 @@ main () __m256i_out = __lasx_xvshuf_h (__m256i_op0, __m256i_op1, __m256i_op2); ASSERTEQ_64 (__LINE__, __m256i_result, __m256i_out); - *((unsigned long *)&__m256i_op0[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op0[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op0[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op0[0]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op1[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op1[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op1[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op1[0]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op2[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op2[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op2[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op2[0]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[0]) = 0x0000000000000000; - __m256i_out = __lasx_xvshuf_h (__m256i_op0, __m256i_op1, __m256i_op2); - ASSERTEQ_64 (__LINE__, __m256i_result, __m256i_out); - - *((unsigned long *)&__m256i_op0[3]) = 0x000000000000fffe; - *((unsigned long *)&__m256i_op0[2]) = 0x00000000000000f0; - *((unsigned long *)&__m256i_op0[1]) = 0x000000000000fffe; - *((unsigned long *)&__m256i_op0[0]) = 0x00000000000000f0; + *((unsigned long *)&__m256i_op0[3]) = 0x000000000000003e; + *((unsigned long *)&__m256i_op0[2]) = 0x0000000000000010; + *((unsigned long *)&__m256i_op0[1]) = 0x000000000000003e; + *((unsigned long *)&__m256i_op0[0]) = 0x0000000000000010; *((unsigned long *)&__m256i_op1[3]) = 0x0000000000000000; *((unsigned long *)&__m256i_op1[2]) = 0x0000000000000000; *((unsigned long *)&__m256i_op1[1]) = 0x0000000000000000; @@ -390,16 +314,16 @@ main () *((unsigned long *)&__m256i_op2[1]) = 0x8000000000000000; *((unsigned long *)&__m256i_op2[0]) = 0x000000ffff88ff88; *((unsigned long *)&__m256i_result[3]) = 0xff88ff88ff880000; - *((unsigned long *)&__m256i_result[2]) = 0xff88ff88ff880000; + *((unsigned long *)&__m256i_result[2]) = 0xff88ff88ff88ff88; *((unsigned long *)&__m256i_result[1]) = 0xff88ff88ff880000; - *((unsigned long *)&__m256i_result[0]) = 0xff88ff88ff880000; + *((unsigned long *)&__m256i_result[0]) = 0xff88ff88ff88ff88; __m256i_out = __lasx_xvshuf_h (__m256i_op0, __m256i_op1, __m256i_op2); ASSERTEQ_64 (__LINE__, __m256i_result, __m256i_out); - *((unsigned long *)&__m256i_op0[3]) = 0x000000010000ffe1; - *((unsigned long *)&__m256i_op0[2]) = 0x0000000101001e18; - *((unsigned long *)&__m256i_op0[1]) = 0x000000010000ffe1; - *((unsigned long *)&__m256i_op0[0]) = 0x0000000101001e18; + *((unsigned long *)&__m256i_op0[3]) = 0x0000000100000011; + *((unsigned long *)&__m256i_op0[2]) = 0x0000000100000018; + *((unsigned long *)&__m256i_op0[1]) = 0x0000000100000001; + *((unsigned long *)&__m256i_op0[0]) = 0x0000000100000008; *((unsigned long *)&__m256i_op1[3]) = 0x98111cca98111cca; *((unsigned long *)&__m256i_op1[2]) = 0x98111cca98111cca; *((unsigned long *)&__m256i_op1[1]) = 0x98111cca98111cca; @@ -408,17 +332,17 @@ main () *((unsigned long *)&__m256i_op2[2]) = 0x0000000101001e18; *((unsigned long *)&__m256i_op2[1]) = 0x000000010000ffe1; *((unsigned long *)&__m256i_op2[0]) = 0x0000000101001e18; - *((unsigned long *)&__m256i_result[3]) = 0x0000000100000000; + *((unsigned long *)&__m256i_result[3]) = 0x0000000100000001; *((unsigned long *)&__m256i_result[2]) = 0x0000000101001e18; - *((unsigned long *)&__m256i_result[1]) = 0x0000000100000000; + *((unsigned long *)&__m256i_result[1]) = 0x0000000100000001; *((unsigned long *)&__m256i_result[0]) = 0x0000000101001e18; __m256i_out = __lasx_xvshuf_w (__m256i_op0, __m256i_op1, __m256i_op2); ASSERTEQ_64 (__LINE__, __m256i_result, __m256i_out); - *((unsigned long *)&__m256i_op0[3]) = 0x0001000100010001; - *((unsigned long *)&__m256i_op0[2]) = 0x80008000b3e8fef1; - *((unsigned long *)&__m256i_op0[1]) = 0x0001000100010001; - *((unsigned long *)&__m256i_op0[0]) = 0x80008000802ea100; + *((unsigned long *)&__m256i_op0[3]) = 0x000000010000001a; + *((unsigned long *)&__m256i_op0[2]) = 0x0000001100000001; + *((unsigned long *)&__m256i_op0[1]) = 0x0000002100000010; + *((unsigned long *)&__m256i_op0[0]) = 0x000000310000001f; *((unsigned long *)&__m256i_op1[3]) = 0x0000000000000000; *((unsigned long *)&__m256i_op1[2]) = 0x0000000000000000; *((unsigned long *)&__m256i_op1[1]) = 0x0000000000000000; @@ -427,17 +351,17 @@ main () *((unsigned long *)&__m256i_op2[2]) = 0x0000000000000002; *((unsigned long *)&__m256i_op2[1]) = 0x0000000000000001; *((unsigned long *)&__m256i_op2[0]) = 0x00000000012e2110; - *((unsigned long *)&__m256i_result[3]) = 0x0000000000000000; + *((unsigned long *)&__m256i_result[3]) = 0x0000000000000001; *((unsigned long *)&__m256i_result[2]) = 0x0000000200000000; - *((unsigned long *)&__m256i_result[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[0]) = 0x012e2110012e2110; + *((unsigned long *)&__m256i_result[1]) = 0x00000000012e2110; + *((unsigned long *)&__m256i_result[0]) = 0x0000000000000000; __m256i_out = __lasx_xvshuf_w (__m256i_op0, __m256i_op1, __m256i_op2); ASSERTEQ_64 (__LINE__, __m256i_result, __m256i_out); - *((unsigned long *)&__m256i_op0[3]) = 0x0000000082a54290; - *((unsigned long *)&__m256i_op0[2]) = 0x00000000028aa700; - *((unsigned long *)&__m256i_op0[1]) = 0x0000000082a54290; - *((unsigned long *)&__m256i_op0[0]) = 0x0000000002a54287; + *((unsigned long *)&__m256i_op0[3]) = 0x0000002f00000000; + *((unsigned long *)&__m256i_op0[2]) = 0x0000001a00000000; + *((unsigned long *)&__m256i_op0[1]) = 0x000000010000001c; + *((unsigned long *)&__m256i_op0[0]) = 0x0000000e0000000c; *((unsigned long *)&__m256i_op1[3]) = 0x0000000000000000; *((unsigned long *)&__m256i_op1[2]) = 0x00000000002a542a; *((unsigned long *)&__m256i_op1[1]) = 0x0000000000000000; @@ -448,8 +372,8 @@ main () *((unsigned long *)&__m256i_op2[0]) = 0x0000000000000000; *((unsigned long *)&__m256i_result[3]) = 0x0000000000000000; *((unsigned long *)&__m256i_result[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[0]) = 0x0000000000000000; + *((unsigned long *)&__m256i_result[1]) = 0x00000000002a542a; + *((unsigned long *)&__m256i_result[0]) = 0x00000000002a542a; __m256i_out = __lasx_xvshuf_w (__m256i_op0, __m256i_op1, __m256i_op2); ASSERTEQ_64 (__LINE__, __m256i_result, __m256i_out); @@ -472,10 +396,10 @@ main () __m256i_out = __lasx_xvshuf_w (__m256i_op0, __m256i_op1, __m256i_op2); ASSERTEQ_64 (__LINE__, __m256i_result, __m256i_out); - *((unsigned long *)&__m256i_op0[3]) = 0xffffffffffffffff; - *((unsigned long *)&__m256i_op0[2]) = 0xffffffffffffffff; - *((unsigned long *)&__m256i_op0[1]) = 0xffffffffffffffff; - *((unsigned long *)&__m256i_op0[0]) = 0xffffffffffffffff; + *((unsigned long *)&__m256i_op0[3]) = 0x0000000100000031; + *((unsigned long *)&__m256i_op0[2]) = 0x0000000100000031; + *((unsigned long *)&__m256i_op0[1]) = 0x0000000100000031; + *((unsigned long *)&__m256i_op0[0]) = 0x0000000100000031; *((unsigned long *)&__m256i_op1[3]) = 0x0000000000000000; *((unsigned long *)&__m256i_op1[2]) = 0x0000000000000000; *((unsigned long *)&__m256i_op1[1]) = 0x0000000000000000; @@ -491,10 +415,10 @@ main () __m256i_out = __lasx_xvshuf_w (__m256i_op0, __m256i_op1, __m256i_op2); ASSERTEQ_64 (__LINE__, __m256i_result, __m256i_out); - *((unsigned long *)&__m256i_op0[3]) = 0x0001000100010001; - *((unsigned long *)&__m256i_op0[2]) = 0x0001000100010001; - *((unsigned long *)&__m256i_op0[1]) = 0x0001000100010001; - *((unsigned long *)&__m256i_op0[0]) = 0x0001000100010001; + *((unsigned long *)&__m256i_op0[3]) = 0x0000000200000001; + *((unsigned long *)&__m256i_op0[2]) = 0x0000000400000003; + *((unsigned long *)&__m256i_op0[1]) = 0x0000000600000005; + *((unsigned long *)&__m256i_op0[0]) = 0x0000000800000007; *((unsigned long *)&__m256i_op1[3]) = 0x000000007fc00000; *((unsigned long *)&__m256i_op1[2]) = 0x000000007fc00000; *((unsigned long *)&__m256i_op1[1]) = 0x000000007fc00000; @@ -504,7 +428,7 @@ main () *((unsigned long *)&__m256i_op2[1]) = 0xdfffffffdfffffff; *((unsigned long *)&__m256i_op2[0]) = 0x8000000080000000; *((unsigned long *)&__m256i_result[3]) = 0x8000000080000000; - *((unsigned long *)&__m256i_result[2]) = 0x8000000080000000; + *((unsigned long *)&__m256i_result[2]) = 0x7fc00000dfffffff; *((unsigned long *)&__m256i_result[1]) = 0x8000000080000000; *((unsigned long *)&__m256i_result[0]) = 0x8000000080000000; __m256i_out = __lasx_xvshuf_w (__m256i_op0, __m256i_op1, __m256i_op2); @@ -530,9 +454,9 @@ main () ASSERTEQ_64 (__LINE__, __m256i_result, __m256i_out); *((unsigned long *)&__m256i_op0[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op0[2]) = 0x0001000104000200; + *((unsigned long *)&__m256i_op0[2]) = 0x0000002000000030; *((unsigned long *)&__m256i_op0[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op0[0]) = 0x0001000104000200; + *((unsigned long *)&__m256i_op0[0]) = 0x0000001000000000; *((unsigned long *)&__m256i_op1[3]) = 0xffffffffffffffff; *((unsigned long *)&__m256i_op1[2]) = 0xffff0000ffff0000; *((unsigned long *)&__m256i_op1[1]) = 0xffffffffffffffff; @@ -586,10 +510,10 @@ main () __m256i_out = __lasx_xvshuf_d (__m256i_op0, __m256i_op1, __m256i_op2); ASSERTEQ_64 (__LINE__, __m256i_result, __m256i_out); - *((unsigned long *)&__m256i_op0[3]) = 0x0000fffffe01fe52; - *((unsigned long *)&__m256i_op0[2]) = 0x00000000ff01ff02; - *((unsigned long *)&__m256i_op0[1]) = 0x0000fffffe01fe52; - *((unsigned long *)&__m256i_op0[0]) = 0x00000000ff01ff02; + *((unsigned long *)&__m256i_op0[3]) = 0x0000000000000000; + *((unsigned long *)&__m256i_op0[2]) = 0x0000000000000001; + *((unsigned long *)&__m256i_op0[1]) = 0x0000000000000002; + *((unsigned long *)&__m256i_op0[0]) = 0x0000000000000003; *((unsigned long *)&__m256i_op1[3]) = 0x0000800000000000; *((unsigned long *)&__m256i_op1[2]) = 0x0000000080008001; *((unsigned long *)&__m256i_op1[1]) = 0x0000800000000000; @@ -598,36 +522,17 @@ main () *((unsigned long *)&__m256i_op2[2]) = 0x000000000000ffff; *((unsigned long *)&__m256i_op2[1]) = 0x0000000000000000; *((unsigned long *)&__m256i_op2[0]) = 0x000000000000ffff; - *((unsigned long *)&__m256i_result[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[2]) = 0x0000000080008001; - *((unsigned long *)&__m256i_result[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[0]) = 0x0000000080008001; - __m256i_out = __lasx_xvshuf_d (__m256i_op0, __m256i_op1, __m256i_op2); - ASSERTEQ_64 (__LINE__, __m256i_result, __m256i_out); - - *((unsigned long *)&__m256i_op0[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op0[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op0[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op0[0]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op1[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op1[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op1[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op1[0]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op2[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op2[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op2[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op2[0]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[3]) = 0x0000000000000000; + *((unsigned long *)&__m256i_result[3]) = 0x000000000000ffff; *((unsigned long *)&__m256i_result[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[0]) = 0x0000000000000000; + *((unsigned long *)&__m256i_result[1]) = 0x0000000080008001; + *((unsigned long *)&__m256i_result[0]) = 0x0000800000000000; __m256i_out = __lasx_xvshuf_d (__m256i_op0, __m256i_op1, __m256i_op2); ASSERTEQ_64 (__LINE__, __m256i_result, __m256i_out); *((unsigned long *)&__m256i_op0[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op0[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op0[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op0[0]) = 0x0000000000000000; + *((unsigned long *)&__m256i_op0[2]) = 0x0000000000000011; + *((unsigned long *)&__m256i_op0[1]) = 0x0000000000000022; + *((unsigned long *)&__m256i_op0[0]) = 0x0000000000000033; *((unsigned long *)&__m256i_op1[3]) = 0x0000000000000000; *((unsigned long *)&__m256i_op1[2]) = 0x0000000000000000; *((unsigned long *)&__m256i_op1[1]) = 0x0000000000000000; @@ -643,44 +548,6 @@ main () __m256i_out = __lasx_xvshuf_d (__m256i_op0, __m256i_op1, __m256i_op2); ASSERTEQ_64 (__LINE__, __m256i_result, __m256i_out); - *((unsigned long *)&__m256i_op0[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op0[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op0[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op0[0]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op1[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op1[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op1[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op1[0]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op2[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op2[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op2[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op2[0]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[0]) = 0x0000000000000000; - __m256i_out = __lasx_xvshuf_d (__m256i_op0, __m256i_op1, __m256i_op2); - ASSERTEQ_64 (__LINE__, __m256i_result, __m256i_out); - - *((unsigned long *)&__m256i_op0[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op0[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op0[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op0[0]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op1[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op1[2]) = 0x0008000000000000; - *((unsigned long *)&__m256i_op1[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op1[0]) = 0x0008000000000000; - *((unsigned long *)&__m256i_op2[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op2[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op2[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op2[0]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[0]) = 0x0000000000000000; - __m256i_out = __lasx_xvshuf_d (__m256i_op0, __m256i_op1, __m256i_op2); - ASSERTEQ_64 (__LINE__, __m256i_result, __m256i_out); - *((unsigned long *)&__m256i_op0[3]) = 0x0000000000000000; *((unsigned long *)&__m256i_op0[2]) = 0x0000000000000000; *((unsigned long *)&__m256i_op0[1]) = 0x0000000000000000; @@ -701,9 +568,9 @@ main () ASSERTEQ_64 (__LINE__, __m256i_result, __m256i_out); *((unsigned long *)&__m256i_op0[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op0[2]) = 0x0000002000000000; - *((unsigned long *)&__m256i_op0[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op0[0]) = 0x0000002000000000; + *((unsigned long *)&__m256i_op0[2]) = 0x0000000000000010; + *((unsigned long *)&__m256i_op0[1]) = 0x0000000000000020; + *((unsigned long *)&__m256i_op0[0]) = 0x0000000000000030; *((unsigned long *)&__m256i_op1[3]) = 0x0000000000000000; *((unsigned long *)&__m256i_op1[2]) = 0x0000000000000000; *((unsigned long *)&__m256i_op1[1]) = 0x0000000000000000; @@ -719,10 +586,10 @@ main () __m256i_out = __lasx_xvshuf_d (__m256i_op0, __m256i_op1, __m256i_op2); ASSERTEQ_64 (__LINE__, __m256i_result, __m256i_out); - *((unsigned long *)&__m256i_op0[3]) = 0xfffeb6839ffffd80; - *((unsigned long *)&__m256i_op0[2]) = 0xfffeb8649d0d6250; - *((unsigned long *)&__m256i_op0[1]) = 0xfffeb6839ffffd80; - *((unsigned long *)&__m256i_op0[0]) = 0xfffeb8649d0d6250; + *((unsigned long *)&__m256i_op0[3]) = 0x000000000000000a; + *((unsigned long *)&__m256i_op0[2]) = 0x000000000000001b; + *((unsigned long *)&__m256i_op0[1]) = 0x000000000000002c; + *((unsigned long *)&__m256i_op0[0]) = 0x000000000000003d; *((unsigned long *)&__m256i_op1[3]) = 0xfffeb6839ffffd80; *((unsigned long *)&__m256i_op1[2]) = 0xfffe97c020010001; *((unsigned long *)&__m256i_op1[1]) = 0xfffeb6839ffffd80; @@ -731,17 +598,17 @@ main () *((unsigned long *)&__m256i_op2[2]) = 0xfffe97c020010001; *((unsigned long *)&__m256i_op2[1]) = 0xfffeb6839ffffd80; *((unsigned long *)&__m256i_op2[0]) = 0xfffe97c020010001; - *((unsigned long *)&__m256i_result[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[0]) = 0x0000000000000000; + *((unsigned long *)&__m256i_result[3]) = 0xfffe97c020010001; + *((unsigned long *)&__m256i_result[2]) = 0xfffeb6839ffffd80; + *((unsigned long *)&__m256i_result[1]) = 0xfffe97c020010001; + *((unsigned long *)&__m256i_result[0]) = 0xfffeb6839ffffd80; __m256i_out = __lasx_xvshuf_d (__m256i_op0, __m256i_op1, __m256i_op2); ASSERTEQ_64 (__LINE__, __m256i_result, __m256i_out); - *((unsigned long *)&__m256i_op0[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op0[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op0[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_op0[0]) = 0x0000000000000000; + *((unsigned long *)&__m256i_op0[3]) = 0x000000000000001a; + *((unsigned long *)&__m256i_op0[2]) = 0x000000000000001b; + *((unsigned long *)&__m256i_op0[1]) = 0x0000000000000002; + *((unsigned long *)&__m256i_op0[0]) = 0x0000000000000007; *((unsigned long *)&__m256i_op1[3]) = 0x0000000000010001; *((unsigned long *)&__m256i_op1[2]) = 0x0000000000010001; *((unsigned long *)&__m256i_op1[1]) = 0x0000000000010001; @@ -750,10 +617,10 @@ main () *((unsigned long *)&__m256i_op2[2]) = 0x0000000000000000; *((unsigned long *)&__m256i_op2[1]) = 0x0000000000000000; *((unsigned long *)&__m256i_op2[0]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[3]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[2]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[1]) = 0x0000000000000000; - *((unsigned long *)&__m256i_result[0]) = 0x0000000000000000; + *((unsigned long *)&__m256i_result[3]) = 0x0000000000010001; + *((unsigned long *)&__m256i_result[2]) = 0x0000000000010001; + *((unsigned long *)&__m256i_result[1]) = 0x0000000000010001; + *((unsigned long *)&__m256i_result[0]) = 0x0000000000010001; __m256i_out = __lasx_xvshuf_d (__m256i_op0, __m256i_op1, __m256i_op2); ASSERTEQ_64 (__LINE__, __m256i_result, __m256i_out); diff --git a/gcc/testsuite/gcc.target/loongarch/vector/lsx/lsx-vshuf.c b/gcc/testsuite/gcc.target/loongarch/vector/lsx/lsx-vshuf.c index 4e7fcc02b12..646935c921a 100644 --- a/gcc/testsuite/gcc.target/loongarch/vector/lsx/lsx-vshuf.c +++ b/gcc/testsuite/gcc.target/loongarch/vector/lsx/lsx-vshuf.c @@ -21,7 +21,7 @@ main () *((unsigned long *)&__m128i_op1[1]) = 0x0000000401000001; *((unsigned long *)&__m128i_op1[0]) = 0x0001000100000004; *((unsigned long *)&__m128i_op2[1]) = 0x0000000000000000; - *((unsigned long *)&__m128i_op2[0]) = 0x00000000007f0000; + *((unsigned long *)&__m128i_op2[0]) = 0x00000000003f0000; *((unsigned long *)&__m128i_result[1]) = 0x0404040404040404; *((unsigned long *)&__m128i_result[0]) = 0x0404040404000404; __m128i_out = __lsx_vshuf_b (__m128i_op0, __m128i_op1, __m128i_op2); @@ -32,7 +32,7 @@ main () *((unsigned long *)&__m128i_op1[1]) = 0xffffffffffffffff; *((unsigned long *)&__m128i_op1[0]) = 0x0000000000000000; *((unsigned long *)&__m128i_op2[1]) = 0x0000000000000000; - *((unsigned long *)&__m128i_op2[0]) = 0xffffffff00000000; + *((unsigned long *)&__m128i_op2[0]) = 0x3f2f1f0f00000000; *((unsigned long *)&__m128i_result[1]) = 0x0000000000000000; *((unsigned long *)&__m128i_result[0]) = 0x0000000000000000; __m128i_out = __lsx_vshuf_b (__m128i_op0, __m128i_op1, __m128i_op2); @@ -64,10 +64,10 @@ main () *((unsigned long *)&__m128i_op0[0]) = 0xffffffffffffffff; *((unsigned long *)&__m128i_op1[1]) = 0x52525252adadadad; *((unsigned long *)&__m128i_op1[0]) = 0x52525252adadadad; - *((unsigned long *)&__m128i_op2[1]) = 0x800000007fffffff; - *((unsigned long *)&__m128i_op2[0]) = 0x800000007fffffff; - *((unsigned long *)&__m128i_result[1]) = 0x00adadad00000000; - *((unsigned long *)&__m128i_result[0]) = 0x00adadad00000000; + *((unsigned long *)&__m128i_op2[1]) = 0x2000000004030201; + *((unsigned long *)&__m128i_op2[0]) = 0x2000000014131211; + *((unsigned long *)&__m128i_result[1]) = 0xadadadad52adadad; + *((unsigned long *)&__m128i_result[0]) = 0xadadadadffffffff; __m128i_out = __lsx_vshuf_b (__m128i_op0, __m128i_op1, __m128i_op2); ASSERTEQ_64 (__LINE__, __m128i_result, __m128i_out); @@ -97,10 +97,10 @@ main () *((unsigned long *)&__m128i_op0[0]) = 0x0000000000000100; *((unsigned long *)&__m128i_op1[1]) = 0x04040403fafafafc; *((unsigned long *)&__m128i_op1[0]) = 0x000000000000ff80; - *((unsigned long *)&__m128i_op2[1]) = 0x0000000000000000; - *((unsigned long *)&__m128i_op2[0]) = 0x0000000000000000; - *((unsigned long *)&__m128i_result[1]) = 0x8080808080808080; - *((unsigned long *)&__m128i_result[0]) = 0x8080808080808080; + *((unsigned long *)&__m128i_op2[1]) = 0x00101a1b1c1d1e1f; + *((unsigned long *)&__m128i_op2[0]) = 0x0807060504030201; + *((unsigned long *)&__m128i_result[1]) = 0x8000020202000000; + *((unsigned long *)&__m128i_result[0]) = 0xfc000000000000ff; __m128i_out = __lsx_vshuf_b (__m128i_op0, __m128i_op1, __m128i_op2); ASSERTEQ_64 (__LINE__, __m128i_result, __m128i_out); @@ -119,10 +119,10 @@ main () *((unsigned long *)&__m128i_op0[0]) = 0xffd7ff8dffa4ff7a; *((unsigned long *)&__m128i_op1[1]) = 0x34947b4b11684f92; *((unsigned long *)&__m128i_op1[0]) = 0xee297a731e5c5f86; - *((unsigned long *)&__m128i_op2[1]) = 0x7fffffffffffffff; - *((unsigned long *)&__m128i_op2[0]) = 0xffc0000000000000; - *((unsigned long *)&__m128i_result[1]) = 0x0000000000000000; - *((unsigned long *)&__m128i_result[0]) = 0x0000868686868686; + *((unsigned long *)&__m128i_op2[1]) = 0x1f0710301a2b332d; + *((unsigned long *)&__m128i_op2[0]) = 0x1f20000000000000; + *((unsigned long *)&__m128i_result[1]) = 0xffee7a7a9811ff7b; + *((unsigned long *)&__m128i_result[0]) = 0xff86868686868686; __m128i_out = __lsx_vshuf_b (__m128i_op0, __m128i_op1, __m128i_op2); ASSERTEQ_64 (__LINE__, __m128i_result, __m128i_out); @@ -137,19 +137,19 @@ main () __m128i_out = __lsx_vshuf_h (__m128i_op0, __m128i_op1, __m128i_op2); ASSERTEQ_64 (__LINE__, __m128i_result, __m128i_out); - *((unsigned long *)&__m128i_op0[1]) = 0xffffffffffffffff; - *((unsigned long *)&__m128i_op0[0]) = 0xffffffffffffffff; + *((unsigned long *)&__m128i_op0[1]) = 0x001f002f003f000f; + *((unsigned long *)&__m128i_op0[0]) = 0x001f002f003f000f; *((unsigned long *)&__m128i_op1[1]) = 0x7fffffffffffffff; *((unsigned long *)&__m128i_op1[0]) = 0x0000000000000000; *((unsigned long *)&__m128i_op2[1]) = 0x0000000000000000; *((unsigned long *)&__m128i_op2[0]) = 0x0000000000000000; - *((unsigned long *)&__m128i_result[1]) = 0x0000000000000000; - *((unsigned long *)&__m128i_result[0]) = 0x0000000000000000; + *((unsigned long *)&__m128i_result[1]) = 0x7fff7fff7fff7fff; + *((unsigned long *)&__m128i_result[0]) = 0x7fff7fff7fff7fff; __m128i_out = __lsx_vshuf_h (__m128i_op0, __m128i_op1, __m128i_op2); ASSERTEQ_64 (__LINE__, __m128i_result, __m128i_out); - *((unsigned long *)&__m128i_op0[1]) = 0x0000000000000000; - *((unsigned long *)&__m128i_op0[0]) = 0x0000000000000000; + *((unsigned long *)&__m128i_op0[1]) = 0x000100040010001f; + *((unsigned long *)&__m128i_op0[0]) = 0x0002000300110012; *((unsigned long *)&__m128i_op1[1]) = 0x0000000000000000; *((unsigned long *)&__m128i_op1[0]) = 0x000000002bfd9461; *((unsigned long *)&__m128i_op2[1]) = 0x00007fff00007fff; @@ -170,74 +170,41 @@ main () __m128i_out = __lsx_vshuf_h (__m128i_op0, __m128i_op1, __m128i_op2); ASSERTEQ_64 (__LINE__, __m128i_result, __m128i_out); - *((unsigned long *)&__m128i_op0[1]) = 0x0000000000000000; - *((unsigned long *)&__m128i_op0[0]) = 0xffffffffffffffff; - *((unsigned long *)&__m128i_op1[1]) = 0x0000000000000000; - *((unsigned long *)&__m128i_op1[0]) = 0x0000000000000000; - *((unsigned long *)&__m128i_op2[1]) = 0x0000000000000000; - *((unsigned long *)&__m128i_op2[0]) = 0x0000000000000000; - *((unsigned long *)&__m128i_result[1]) = 0x0000000000000000; - *((unsigned long *)&__m128i_result[0]) = 0x0000000000000000; - __m128i_out = __lsx_vshuf_h (__m128i_op0, __m128i_op1, __m128i_op2); - ASSERTEQ_64 (__LINE__, __m128i_result, __m128i_out); - - *((unsigned long *)&__m128i_op0[1]) = 0x000300037ff000ff; - *((unsigned long *)&__m128i_op0[0]) = 0x0003000300a10003; + *((unsigned long *)&__m128i_op0[1]) = 0x000300030000001f; + *((unsigned long *)&__m128i_op0[0]) = 0x0003000300000003; *((unsigned long *)&__m128i_op1[1]) = 0x000300037ff000ff; *((unsigned long *)&__m128i_op1[0]) = 0x0003000300a10003; *((unsigned long *)&__m128i_op2[1]) = 0x000000007ff000ff; *((unsigned long *)&__m128i_op2[0]) = 0x0000000000000000; - *((unsigned long *)&__m128i_result[1]) = 0x0000000000000000; + *((unsigned long *)&__m128i_result[1]) = 0x0000000000000003; *((unsigned long *)&__m128i_result[0]) = 0x0000000000000000; __m128i_out = __lsx_vshuf_h (__m128i_op0, __m128i_op1, __m128i_op2); ASSERTEQ_64 (__LINE__, __m128i_result, __m128i_out); - *((unsigned long *)&__m128i_op0[1]) = 0x0909000009090000; - *((unsigned long *)&__m128i_op0[0]) = 0x0909000009090000; + *((unsigned long *)&__m128i_op0[1]) = 0x0019000000090000; + *((unsigned long *)&__m128i_op0[0]) = 0x0019000000090000; *((unsigned long *)&__m128i_op1[1]) = 0x0909000009090000; *((unsigned long *)&__m128i_op1[0]) = 0x0909000009090000; *((unsigned long *)&__m128i_op2[1]) = 0x002a05a2f059094a; *((unsigned long *)&__m128i_op2[0]) = 0x05ad3ba576eae048; - *((unsigned long *)&__m128i_result[1]) = 0x0909e0480909e048; - *((unsigned long *)&__m128i_result[0]) = 0x0909e0480909e048; - __m128i_out = __lsx_vshuf_h (__m128i_op0, __m128i_op1, __m128i_op2); - ASSERTEQ_64 (__LINE__, __m128i_result, __m128i_out); - - *((unsigned long *)&__m128i_op0[1]) = 0x0000000000000000; - *((unsigned long *)&__m128i_op0[0]) = 0x0000000000000000; - *((unsigned long *)&__m128i_op1[1]) = 0x0000000000000000; - *((unsigned long *)&__m128i_op1[0]) = 0x0000000000000000; - *((unsigned long *)&__m128i_op2[1]) = 0x0000000000000000; - *((unsigned long *)&__m128i_op2[0]) = 0x0000000000000000; - *((unsigned long *)&__m128i_result[1]) = 0x0000000000000000; - *((unsigned long *)&__m128i_result[0]) = 0x0000000000000000; + *((unsigned long *)&__m128i_result[1]) = 0x909e0480909e048; + *((unsigned long *)&__m128i_result[0]) = 0x909e0480909e048; __m128i_out = __lsx_vshuf_h (__m128i_op0, __m128i_op1, __m128i_op2); ASSERTEQ_64 (__LINE__, __m128i_result, __m128i_out); - *((unsigned long *)&__m128i_op0[1]) = 0x00000000000000c0; - *((unsigned long *)&__m128i_op0[0]) = 0x00000001ffffff29; + *((unsigned long *)&__m128i_op0[1]) = 0x0000000000000030; + *((unsigned long *)&__m128i_op0[0]) = 0x0000000000000029; *((unsigned long *)&__m128i_op1[1]) = 0x0000000000000000; *((unsigned long *)&__m128i_op1[0]) = 0x0000000000000000; *((unsigned long *)&__m128i_op2[1]) = 0x00000000000000c0; *((unsigned long *)&__m128i_op2[0]) = 0x00000001ffffff29; - *((unsigned long *)&__m128i_result[1]) = 0xffffff2900000000; + *((unsigned long *)&__m128i_result[1]) = 0xffffff29ffffff29; *((unsigned long *)&__m128i_result[0]) = 0x0000000100000001; __m128i_out = __lsx_vshuf_w (__m128i_op0, __m128i_op1, __m128i_op2); ASSERTEQ_64 (__LINE__, __m128i_result, __m128i_out); *((unsigned long *)&__m128i_op0[1]) = 0x0000000000000000; - *((unsigned long *)&__m128i_op0[0]) = 0x0000000000000000; - *((unsigned long *)&__m128i_op1[1]) = 0x0000000000000000; - *((unsigned long *)&__m128i_op1[0]) = 0x0000000000000000; - *((unsigned long *)&__m128i_op2[1]) = 0x0000000000000000; - *((unsigned long *)&__m128i_op2[0]) = 0x0000000000000000; - *((unsigned long *)&__m128i_result[1]) = 0x0000000000000000; - *((unsigned long *)&__m128i_result[0]) = 0x0000000000000000; - __m128i_out = __lsx_vshuf_w (__m128i_op0, __m128i_op1, __m128i_op2); - ASSERTEQ_64 (__LINE__, __m128i_result, __m128i_out); - - *((unsigned long *)&__m128i_op0[1]) = 0x0000000000000000; - *((unsigned long *)&__m128i_op0[0]) = 0x00000000000000ff; + *((unsigned long *)&__m128i_op0[0]) = 0x000000000000001f; *((unsigned long *)&__m128i_op1[1]) = 0x0000000000000000; *((unsigned long *)&__m128i_op1[0]) = 0x1f54e0ab00000000; *((unsigned long *)&__m128i_op2[1]) = 0x0101010101010101; @@ -247,19 +214,8 @@ main () __m128i_out = __lsx_vshuf_w (__m128i_op0, __m128i_op1, __m128i_op2); ASSERTEQ_64 (__LINE__, __m128i_result, __m128i_out); - *((unsigned long *)&__m128i_op0[1]) = 0x0000000000000000; - *((unsigned long *)&__m128i_op0[0]) = 0x0000000000000000; - *((unsigned long *)&__m128i_op1[1]) = 0x0000000000000000; - *((unsigned long *)&__m128i_op1[0]) = 0x0000000000000000; - *((unsigned long *)&__m128i_op2[1]) = 0x0000000000000000; - *((unsigned long *)&__m128i_op2[0]) = 0x0000000000000000; - *((unsigned long *)&__m128i_result[1]) = 0x0000000000000000; - *((unsigned long *)&__m128i_result[0]) = 0x0000000000000000; - __m128i_out = __lsx_vshuf_w (__m128i_op0, __m128i_op1, __m128i_op2); - ASSERTEQ_64 (__LINE__, __m128i_result, __m128i_out); - - *((unsigned long *)&__m128i_op0[1]) = 0x0000000000007fff; - *((unsigned long *)&__m128i_op0[0]) = 0x0000000000000000; + *((unsigned long *)&__m128i_op0[1]) = 0x0000002f0000002f; + *((unsigned long *)&__m128i_op0[0]) = 0x0000001000000000; *((unsigned long *)&__m128i_op1[1]) = 0x0000000000000000; *((unsigned long *)&__m128i_op1[0]) = 0x0000000000000000; *((unsigned long *)&__m128i_op2[1]) = 0x0000000020000020; @@ -280,30 +236,30 @@ main () __m128i_out = __lsx_vshuf_w (__m128i_op0, __m128i_op1, __m128i_op2); ASSERTEQ_64 (__LINE__, __m128i_result, __m128i_out); - *((unsigned long *)&__m128i_op0[1]) = 0x0000000000000000; - *((unsigned long *)&__m128i_op0[0]) = 0x0000000004870ba0; + *((unsigned long *)&__m128i_op0[1]) = 0x0000000900000010; + *((unsigned long *)&__m128i_op0[0]) = 0x0000002000000003; *((unsigned long *)&__m128i_op1[1]) = 0x0000000000000000; *((unsigned long *)&__m128i_op1[0]) = 0x0000001000000010; *((unsigned long *)&__m128i_op2[1]) = 0x8000000100000000; *((unsigned long *)&__m128i_op2[0]) = 0x8000000000000103; *((unsigned long *)&__m128i_result[1]) = 0x0000010300000103; - *((unsigned long *)&__m128i_result[0]) = 0x0000010300000000; + *((unsigned long *)&__m128i_result[0]) = 0x0000010380000001; __m128i_out = __lsx_vshuf_w (__m128i_op0, __m128i_op1, __m128i_op2); ASSERTEQ_64 (__LINE__, __m128i_result, __m128i_out); - *((unsigned long *)&__m128i_op0[1]) = 0x000000ff0000857a; - *((unsigned long *)&__m128i_op0[0]) = 0x05fafe0101fe000e; + *((unsigned long *)&__m128i_op0[1]) = 0x0000001000000007; + *((unsigned long *)&__m128i_op0[0]) = 0x0000002000000001; *((unsigned long *)&__m128i_op1[1]) = 0x0000000000000000; *((unsigned long *)&__m128i_op1[0]) = 0x0000000000000000; *((unsigned long *)&__m128i_op2[1]) = 0xffffffffffffffff; *((unsigned long *)&__m128i_op2[0]) = 0xffffffffffffffff; *((unsigned long *)&__m128i_result[1]) = 0x0000000000000000; - *((unsigned long *)&__m128i_result[0]) = 0xffffffff00000000; + *((unsigned long *)&__m128i_result[0]) = 0xffffffffffffffff; __m128i_out = __lsx_vshuf_w (__m128i_op0, __m128i_op1, __m128i_op2); ASSERTEQ_64 (__LINE__, __m128i_result, __m128i_out); - *((unsigned long *)&__m128i_op0[1]) = 0xada4808924882588; - *((unsigned long *)&__m128i_op0[0]) = 0xacad25090caca5a4; + *((unsigned long *)&__m128i_op0[1]) = 0x0000001a0000001b; + *((unsigned long *)&__m128i_op0[0]) = 0x0000000a0000000b; *((unsigned long *)&__m128i_op1[1]) = 0x021b7d24c9678a35; *((unsigned long *)&__m128i_op1[0]) = 0x030298a6a1030a49; *((unsigned long *)&__m128i_op2[1]) = 0x0000000000000000; @@ -313,8 +269,8 @@ main () __m128i_out = __lsx_vshuf_w (__m128i_op0, __m128i_op1, __m128i_op2); ASSERTEQ_64 (__LINE__, __m128i_result, __m128i_out); - *((unsigned long *)&__m128i_op0[1]) = 0x00000000ffffffff; - *((unsigned long *)&__m128i_op0[0]) = 0xffffffffffffffff; + *((unsigned long *)&__m128i_op0[1]) = 0x0000000000000003; + *((unsigned long *)&__m128i_op0[0]) = 0x0000000000000013; *((unsigned long *)&__m128i_op1[1]) = 0x0000000000000000; *((unsigned long *)&__m128i_op1[0]) = 0x0000000000000000; *((unsigned long *)&__m128i_op2[1]) = 0x0000000000000000; @@ -324,14 +280,14 @@ main () __m128i_out = __lsx_vshuf_d (__m128i_op0, __m128i_op1, __m128i_op2); ASSERTEQ_64 (__LINE__, __m128i_result, __m128i_out); - *((unsigned long *)&__m128i_op0[1]) = 0xdfa6e0c6d46cdc13; - *((unsigned long *)&__m128i_op0[0]) = 0x21fc7081ec69b5f2; + *((unsigned long *)&__m128i_op0[1]) = 0x0000000000000001; + *((unsigned long *)&__m128i_op0[0]) = 0x0000000000000011; *((unsigned long *)&__m128i_op1[1]) = 0x0000000000000000; *((unsigned long *)&__m128i_op1[0]) = 0x000000002c002400; *((unsigned long *)&__m128i_op2[1]) = 0xffffb96bffff57c9; *((unsigned long *)&__m128i_op2[0]) = 0xffff6080ffff4417; - *((unsigned long *)&__m128i_result[1]) = 0x0000000000000000; - *((unsigned long *)&__m128i_result[0]) = 0x0000000000000000; + *((unsigned long *)&__m128i_result[1]) = 0xffffb96bffff57c9; + *((unsigned long *)&__m128i_result[0]) = 0xffffb96bffff57c9; __m128i_out = __lsx_vshuf_d (__m128i_op0, __m128i_op1, __m128i_op2); ASSERTEQ_64 (__LINE__, __m128i_result, __m128i_out); @@ -346,8 +302,8 @@ main () __m128i_out = __lsx_vshuf_d (__m128i_op0, __m128i_op1, __m128i_op2); ASSERTEQ_64 (__LINE__, __m128i_result, __m128i_out); - *((unsigned long *)&__m128i_op0[1]) = 0x0000000000000000; - *((unsigned long *)&__m128i_op0[0]) = 0x0000000000000000; + *((unsigned long *)&__m128i_op0[1]) = 0x0000000000000020; + *((unsigned long *)&__m128i_op0[0]) = 0x0000000000000010; *((unsigned long *)&__m128i_op1[1]) = 0x0000000000002000; *((unsigned long *)&__m128i_op1[0]) = 0xf0003000f0003000; *((unsigned long *)&__m128i_op2[1]) = 0x0000000000000000; @@ -357,30 +313,30 @@ main () __m128i_out = __lsx_vshuf_d (__m128i_op0, __m128i_op1, __m128i_op2); ASSERTEQ_64 (__LINE__, __m128i_result, __m128i_out); - *((unsigned long *)&__m128i_op0[1]) = 0x021b7d2449678a35; - *((unsigned long *)&__m128i_op0[0]) = 0x030298a621030a49; + *((unsigned long *)&__m128i_op0[1]) = 0x0000000000000007; + *((unsigned long *)&__m128i_op0[0]) = 0x000000000000001a; *((unsigned long *)&__m128i_op1[1]) = 0x0000000000000000; *((unsigned long *)&__m128i_op1[0]) = 0x7fff7fff7fff7fff; *((unsigned long *)&__m128i_op2[1]) = 0x021b7d24c9678a35; *((unsigned long *)&__m128i_op2[0]) = 0x030298a6a1030a49; - *((unsigned long *)&__m128i_result[1]) = 0x021b7d24c9678a35; - *((unsigned long *)&__m128i_result[0]) = 0x0000000000000000; + *((unsigned long *)&__m128i_result[1]) = 0x0000000000000000; + *((unsigned long *)&__m128i_result[0]) = 0x7fff7fff7fff7fff; __m128i_out = __lsx_vshuf_d (__m128i_op0, __m128i_op1, __m128i_op2); ASSERTEQ_64 (__LINE__, __m128i_result, __m128i_out); - *((unsigned long *)&__m128i_op0[1]) = 0x7f7f00007f7f0000; - *((unsigned long *)&__m128i_op0[0]) = 0x7f7f80807f7f8080; + *((unsigned long *)&__m128i_op0[1]) = 0x0000000000000002; + *((unsigned long *)&__m128i_op0[0]) = 0x0000000000000001; *((unsigned long *)&__m128i_op1[1]) = 0x0000000000000000; *((unsigned long *)&__m128i_op1[0]) = 0x0000fffe0000fffe; *((unsigned long *)&__m128i_op2[1]) = 0x7f8000007f800000; *((unsigned long *)&__m128i_op2[0]) = 0x7f8000007f800000; - *((unsigned long *)&__m128i_result[1]) = 0x7f8000007f800000; - *((unsigned long *)&__m128i_result[0]) = 0x0000000000000000; + *((unsigned long *)&__m128i_result[1]) = 0x0000fffe0000fffe; + *((unsigned long *)&__m128i_result[0]) = 0x7f8000007f800000; __m128i_out = __lsx_vshuf_d (__m128i_op0, __m128i_op1, __m128i_op2); ASSERTEQ_64 (__LINE__, __m128i_result, __m128i_out); - *((unsigned long *)&__m128i_op0[1]) = 0xffffffffffffffff; - *((unsigned long *)&__m128i_op0[0]) = 0xfffffffffff10000; + *((unsigned long *)&__m128i_op0[1]) = 0x0000000000000010; + *((unsigned long *)&__m128i_op0[0]) = 0x0000000000000020; *((unsigned long *)&__m128i_op1[1]) = 0x0000000000000000; *((unsigned long *)&__m128i_op1[0]) = 0x0000000000000000; *((unsigned long *)&__m128i_op2[1]) = 0x0000000000000000;