From patchwork Fri Nov 20 16:11:57 2015 Content-Type: text/plain; charset="utf-8" MIME-Version: 1.0 Content-Transfer-Encoding: 7bit X-Patchwork-Submitter: Yao Qi X-Patchwork-Id: 9759 Received: (qmail 42942 invoked by alias); 20 Nov 2015 16:12:18 -0000 Mailing-List: contact gdb-patches-help@sourceware.org; run by ezmlm Precedence: bulk List-Id: List-Unsubscribe: List-Subscribe: List-Archive: List-Post: List-Help: , Sender: gdb-patches-owner@sourceware.org Delivered-To: mailing list gdb-patches@sourceware.org Received: (qmail 42532 invoked by uid 89); 20 Nov 2015 16:12:17 -0000 Authentication-Results: sourceware.org; auth=none X-Virus-Found: No X-Spam-SWARE-Status: No, score=-2.3 required=5.0 tests=AWL, BAYES_00, FREEMAIL_FROM, RCVD_IN_DNSWL_LOW, SPF_PASS autolearn=ham version=3.3.2 X-HELO: mail-pa0-f50.google.com Received: from mail-pa0-f50.google.com (HELO mail-pa0-f50.google.com) (209.85.220.50) by sourceware.org (qpsmtpd/0.93/v0.84-503-g423c35a) with (AES128-GCM-SHA256 encrypted) ESMTPS; Fri, 20 Nov 2015 16:12:08 +0000 Received: by padhx2 with SMTP id hx2so120501560pad.1 for ; Fri, 20 Nov 2015 08:12:06 -0800 (PST) X-Received: by 10.68.136.2 with SMTP id pw2mr7597908pbb.20.1448035926831; Fri, 20 Nov 2015 08:12:06 -0800 (PST) Received: from E107787-LIN.cambridge.arm.com (gcc1-power7.osuosl.org. [140.211.15.137]) by smtp.gmail.com with ESMTPSA id ws6sm230974pbc.33.2015.11.20.08.12.05 for (version=TLS1_2 cipher=ECDHE-RSA-AES128-SHA bits=128/128); Fri, 20 Nov 2015 08:12:06 -0800 (PST) From: Yao Qi X-Google-Original-From: Yao Qi To: gdb-patches@sourceware.org Subject: [PATCH 3/3] New test gdb.arch/arm-neon.exp Date: Fri, 20 Nov 2015 16:11:57 +0000 Message-Id: <1448035917-3049-4-git-send-email-yao.qi@linaro.org> In-Reply-To: <1448035917-3049-1-git-send-email-yao.qi@linaro.org> References: <1448035917-3049-1-git-send-email-yao.qi@linaro.org> X-IsSubscribed: yes Both ARM and AArch64 have defined some SIMD data types in arm_neon.h, but we don't have a test case for passing them and returning them in inferior call. This test also covers passing and returning homogeneous short vector aggregate (defined by AArch64 ABI document) in inferior call too. gdb/testsuite: * gdb.arch/arm-neon.exp: New. * gdb.arch/arm-neon.c: New. --- gdb/testsuite/gdb.arch/arm-neon.c | 102 ++++++++++++++++++++++++++++++++++++ gdb/testsuite/gdb.arch/arm-neon.exp | 62 ++++++++++++++++++++++ 2 files changed, 164 insertions(+) create mode 100644 gdb/testsuite/gdb.arch/arm-neon.c create mode 100644 gdb/testsuite/gdb.arch/arm-neon.exp diff --git a/gdb/testsuite/gdb.arch/arm-neon.c b/gdb/testsuite/gdb.arch/arm-neon.c new file mode 100644 index 0000000..e1fdd34 --- /dev/null +++ b/gdb/testsuite/gdb.arch/arm-neon.c @@ -0,0 +1,102 @@ +/* Copyright 2015 Free Software Foundation, Inc. + + This file is part of GDB. + + This program is free software; you can redistribute it and/or modify + it under the terms of the GNU General Public License as published by + the Free Software Foundation; either version 3 of the License, or + (at your option) any later version. + + This program is distributed in the hope that it will be useful, + but WITHOUT ANY WARRANTY; without even the implied warranty of + MERCHANTABILITY or FITNESS FOR A PARTICULAR PURPOSE. See the + GNU General Public License for more details. + + You should have received a copy of the GNU General Public License + along with this program. If not, see . */ + +#include + +#define DEF_FUNC1(N, TYPE, VALUE...) \ + TYPE a##N = {VALUE}; \ + TYPE vec_func##N(TYPE a) \ + { return a; } + +/* 64-bit vector. */ + +DEF_FUNC1(1, int8x8_t, -1, -2, 3, 4, 5, -6, 7, 8) +DEF_FUNC1(2, int16x4_t, 0, 2, -4, 6) +DEF_FUNC1(3, int32x2_t, -10, 12) +DEF_FUNC1(4, uint8x8_t, 1, 2, 3, 4, 5, 6, 7, 8) +DEF_FUNC1(5, uint16x4_t, 4, 3, 2, 1) +DEF_FUNC1(6, uint32x2_t, 100, 200) +DEF_FUNC1(7, float32x2_t, 1.0, 2.0) +DEF_FUNC1(8, poly8x8_t, 8, 10, 12, 14, 15, 16, 1, 0) +DEF_FUNC1(9, poly16x4_t, 32, 33, 34, 35) + +/* 128-bit vector. */ + +DEF_FUNC1(10, int8x16_t, -1, -2, 3, 4, 5, -6, 7, 8, 8, 10, 12, 14, 15, 16, 1, 0); +DEF_FUNC1(11, int16x8_t, 4, 10, -13, -16, 18, 1, 2, 4); +DEF_FUNC1(12, int32x4_t, 32, 33, -34, 35); +DEF_FUNC1(13, uint8x16_t, 1, 2, 3, 4, 5, 6, 7, 8, 8, 10, 12, 14, 15, 16, 1, 0); +DEF_FUNC1(14, uint16x8_t, 4, 10, 13, 16, 18, 1, 2, 4); +DEF_FUNC1(15, uint32x4_t, 16, 18, 1, 2); +DEF_FUNC1(16, float32x4_t, 2.0, 5.0, 4.0, 8.0); +DEF_FUNC1(17, poly8x16_t, 8, 10, 12, 14, 15, 16, 1, 0, 8, 10, 12, 14, 15, 16, 1, 0); +DEF_FUNC1(18, poly16x8_t, 8, 10, 12, 14, 15, 16, 1, 0); + +/* Homogeneous Short Vector Aggregate. */ + +struct hva1 +{ + int8x8_t f1; + int8x8_t f2; + int8x8_t f3; +}; + +struct hva2 +{ + int8x8_t f1; + int16x4_t f2; + int32x2_t f3; +}; + +struct hva3 +{ + int8x8_t f1; + int8x8_t f2; + int8x8_t f3; + int8x8_t f4; + int16x4_t f5; + int32x2_t f6; +}; + +struct hva1 hva1 = {{-1, -2, 3, 4, 5, -6, 7, 8}, + {-1, -2, 3, 4, 5, -6, 7, 8}, + {-1, -2, 3, 4, 5, -6, 7, 8}}; + +struct hva2 hva2 = {{-1, -2, 3, 4, 5, -6, 7, 8}, + {0, 2, -4, 6}, + {-10, 12}}; + +struct hva3 hva3 = {{-1, -2, 3, 4, 5, -6, 7, 8}, + {-1, -2, 3, 4, 5, -6, 7, 8}, + {-1, -2, 3, 4, 5, -6, 7, 8}, + {-1, -2, 3, 4, 5, -6, 7, 8}, + {0, 2, -4, 6}, + {-10, 12}}; + +#define DEF_FUNC2(N) \ + struct hva##N hva_func##N(struct hva##N a) \ + { return a; } + +DEF_FUNC2 (1) +DEF_FUNC2 (2) +DEF_FUNC2 (3) + +int +main (void) +{ + return 0; +} diff --git a/gdb/testsuite/gdb.arch/arm-neon.exp b/gdb/testsuite/gdb.arch/arm-neon.exp new file mode 100644 index 0000000..b64a90b --- /dev/null +++ b/gdb/testsuite/gdb.arch/arm-neon.exp @@ -0,0 +1,62 @@ +# Copyright 2015 Free Software Foundation, Inc. + +# This program is free software; you can redistribute it and/or modify +# it under the terms of the GNU General Public License as published by +# the Free Software Foundation; either version 3 of the License, or +# (at your option) any later version. +# +# This program is distributed in the hope that it will be useful, +# but WITHOUT ANY WARRANTY; without even the implied warranty of +# MERCHANTABILITY or FITNESS FOR A PARTICULAR PURPOSE. See the +# GNU General Public License for more details. +# +# You should have received a copy of the GNU General Public License +# along with this program. If not, see . + +# This file is part of the gdb testsuite. + +if {![istarget "aarch64*-*-*"] && ![istarget "arm*-*-*"]} { + verbose "Skipping ${gdb_test_file_name}." + return +} + +standard_testfile +if { [prepare_for_testing ${testfile}.exp ${testfile} ${srcfile}] } { + unsupported "ARM NEON is not supported" + return -1 +} + +if ![runto_main] { + untested "could not run to main" + return -1 +} + +# Test passing vectors in function argument in the inferior call. + +for {set i 1} {$i <= 18} {incr i} { + + set contents "" + set test "print a${i}" + gdb_test_multiple "p a${i}" $test { + -re " = (.*)\r\n$gdb_prompt $" { + set contents $expect_out(1,string) + } + } + regsub -all "\{" $contents "\\\\\{" contents + gdb_test "p vec_func${i} \(a${i}\)" "= $contents" +} + +# Test passing homogeneous vector aggregate in function argument +# in the inferior call. + +for {set i 1} {$i <= 3} {incr i} { + set contents "" + set test "print hva${i}" + gdb_test_multiple "p hva${i}" $test { + -re " = (.*)\r\n$gdb_prompt $" { + set contents $expect_out(1,string) + } + } + regsub -all "\{" $contents "\\\\\{" contents + gdb_test "p hva_func${i} \(hva${i}\)" "= $contents" +}