From mboxrd@z Thu Jan 1 00:00:00 1970 Return-Path: Received: from simark.ca by simark.ca with LMTP id 2RVGEhV4fGpXmCAAWB0awg (envelope-from ) for ; Wed, 12 Aug 2026 09:41:41 -0400 Authentication-Results: simark.ca; dkim=pass (2048-bit key; unprotected) header.d=intel.com header.i=@intel.com header.a=rsa-sha256 header.s=Intel header.b=ZcBbn6Zb; dkim-atps=neutral Received: by simark.ca (Postfix, from userid 112) id 45AA11E033; Wed, 12 Aug 2026 09:41:41 -0400 (EDT) X-Spam-Checker-Version: SpamAssassin 4.0.1 (2024-03-25) on simark.ca X-Spam-Level: X-Spam-Status: No, score=-6.4 required=5.0 tests=ARC_SIGNED,ARC_VALID,BAYES_00, DKIMWL_WL_HIGH,DKIM_SIGNED,DKIM_VALID,DKIM_VALID_AU,MAILING_LIST_MULTI, RCVD_IN_DNSWL_MED autolearn=ham autolearn_force=no version=4.0.1 Received: from vm01.sourceware.org (vm01.sourceware.org [38.145.34.32]) (using TLSv1.3 with cipher TLS_AES_256_GCM_SHA384 (256/256 bits) key-exchange x25519 server-signature ECDSA (prime256v1) server-digest SHA256) (No client certificate requested) by simark.ca (Postfix) with ESMTPS id 80E481E033 for ; Wed, 12 Aug 2026 09:41:40 -0400 (EDT) Received: from vm01.sourceware.org (localhost [IPv6:::1]) by sourceware.org (Postfix) with ESMTP id 27D5E4BA79BE for ; Wed, 12 Aug 2026 13:41:40 +0000 (GMT) DKIM-Filter: OpenDKIM Filter v2.11.0 sourceware.org 27D5E4BA79BE Authentication-Results: sourceware.org; dkim=pass (2048-bit key, unprotected) header.d=intel.com header.i=@intel.com header.a=rsa-sha256 header.s=Intel header.b=ZcBbn6Zb Received: from mgamail.intel.com (mgamail.intel.com [192.198.163.12]) by sourceware.org (Postfix) with ESMTPS id 529764BA23E4 for ; Wed, 12 Aug 2026 13:30:20 +0000 (GMT) DMARC-Filter: OpenDMARC Filter v1.4.2 sourceware.org 529764BA23E4 Authentication-Results: sourceware.org; dmarc=pass (p=none dis=none) header.from=intel.com Authentication-Results: sourceware.org; spf=pass smtp.mailfrom=intel.com ARC-Filter: OpenARC Filter v1.0.0 sourceware.org 529764BA23E4 Authentication-Results: sourceware.org; arc=none smtp.remote-ip=192.198.163.12 ARC-Seal: i=1; a=rsa-sha256; d=sourceware.org; s=key; t=1786541420; cv=none; b=i1szwxGVgBpCjvRJvpeHbWkMb5yLnvTgtUUAfb+PbjewkDmCgibg0CZJBbyS3dHATMhdp3WE4ZnALo899YGQS5aTiRAOuQv4NR6uBWTrZs8fTuVVxHZzWnw7Usts4jg+oW8s9pn5du1cp5dET4NGd8JAkdtll2hDNSjCiS2Nk88= ARC-Message-Signature: i=1; a=rsa-sha256; d=sourceware.org; s=key; t=1786541420; c=relaxed/simple; bh=lPouY4nnMtUt4lWIeJAji/Deg1Iw0ZqDAFopAsk785s=; h=DKIM-Signature:From:To:Subject:Date:Message-ID:MIME-Version; b=koZu1w2AScbPgl165V+89dMu8jgmtwCV+iTVkQtsobN7e5U5JGpAb94eNPW7OT4Poar+zcG6J2bpOVDIxTHNXLTCox6lsYEM3sIoeJ8w6oDAAwF8ejTFg8ACAsbKCmoKntR59ViRWHPfSmKM+VU1l7XhUrEn8Dv3US9U1iHjaN4= ARC-Authentication-Results: i=1; sourceware.org; dkim=pass (2048-bit key, unprotected) header.d=intel.com header.i=@intel.com header.a=rsa-sha256 header.s=Intel header.b=ZcBbn6Zb DKIM-Filter: OpenDKIM Filter v2.11.0 sourceware.org 529764BA23E4 DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/simple; d=intel.com; i=@intel.com; q=dns/txt; s=Intel; t=1786541420; x=1818077420; h=from:to:cc:subject:date:message-id:in-reply-to: references:mime-version:content-transfer-encoding; bh=lPouY4nnMtUt4lWIeJAji/Deg1Iw0ZqDAFopAsk785s=; b=ZcBbn6Zbb1qWzGesCMoJTd7ccovyX56GZF0P2jJJB/JFj6GnfMjzaZD9 YNZpgzCiUxus2+L7zXav5thOQvmciumVErWX91Aq7hj8CiTHq00MqBggy Q2kOLzI8Ajj/M++IrVWSN7ccfvGZn+d8wZf4y0GWcxb0Mv5T+4OFVsqQ9 2PtH/EKLbDxX5/K14M/aUYIdV7jRcMWet+RvtZBPLjasoWsgpYb7e9ZPx vudCbUThP9zHFV9lF5YrKzE80ElUrPvpvJqx76+V/Bkewsj//A/Ej53Ay XH7clQJkQ8OpJAOn8N7OlSuOq6Z3SKC8Z5+jNFLFkffkKFtvbA7qSxJQ7 A==; X-CSE-ConnectionGUID: 6G+8AbmoSy+GJdIZUg/ESQ== X-CSE-MsgGUID: yO6Nn4U0SIuEigngXGXkSQ== X-IronPort-AV: E=McAfee;i="6800,10657,11872"; a="90910802" X-IronPort-AV: E=Sophos;i="6.25,219,1779174000"; d="scan'208";a="90910802" Received: from fmviesa005.fm.intel.com ([10.60.135.145]) by fmvoesa106.fm.intel.com with ESMTP/TLS/ECDHE-RSA-AES256-GCM-SHA384; 12 Aug 2026 06:30:19 -0700 X-CSE-ConnectionGUID: 39ltraBrR++oVFzX7Mg9mg== X-CSE-MsgGUID: W7kqV3VaTyaAF0iYcFuCfw== X-ExtLoop1: 1 X-IronPort-AV: E=Sophos;i="6.25,219,1779174000"; d="scan'208";a="268804840" Received: from gkldtt-dev-004.igk.intel.com (HELO localhost) ([10.123.221.202]) by fmviesa005-auth.fm.intel.com with ESMTP/TLS/ECDHE-RSA-AES256-GCM-SHA384; 12 Aug 2026 06:30:18 -0700 From: Markus Metzger To: gdb-patches@sourceware.org Cc: Albertano Caruso Subject: [PATCH v4 42/44] testsuite, arch, intelgt: add a disassembly test Date: Wed, 12 Aug 2026 15:28:02 +0200 Message-ID: <20260812132805.380163-43-markus.t.metzger@intel.com> X-Mailer: git-send-email 2.53.0 In-Reply-To: <20260812132805.380163-1-markus.t.metzger@intel.com> References: <20260812132805.380163-1-markus.t.metzger@intel.com> MIME-Version: 1.0 Content-Type: text/plain; charset="us-ascii" Content-Transfer-Encoding: 7bit X-BeenThere: gdb-patches@sourceware.org X-Mailman-Version: 2.1.30 Precedence: list List-Id: Gdb-patches mailing list List-Unsubscribe: , List-Archive: List-Post: List-Help: List-Subscribe: , Errors-To: gdb-patches-bounces~public-inbox=simark.ca@sourceware.org From: Albertano Caruso Test the disassemble command on the Intel GT target. --- .../gdb.arch/intelgt-disassemble.exp | 82 +++++++++++++++++++ gdb/testsuite/gdb.arch/sycl-hello.cpp | 33 ++++++++ 2 files changed, 115 insertions(+) create mode 100644 gdb/testsuite/gdb.arch/intelgt-disassemble.exp create mode 100644 gdb/testsuite/gdb.arch/sycl-hello.cpp diff --git a/gdb/testsuite/gdb.arch/intelgt-disassemble.exp b/gdb/testsuite/gdb.arch/intelgt-disassemble.exp new file mode 100644 index 00000000000..f3c3dc8b600 --- /dev/null +++ b/gdb/testsuite/gdb.arch/intelgt-disassemble.exp @@ -0,0 +1,82 @@ +# Copyright 2019-2026 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 . +# +# Tests disassembly support for Intel(R) Graphics Technology. + +load_lib sycl.exp + +standard_testfile sycl-hello.cpp + +set sycl_device_list [init_sycl_devices_list] +if {[llength $sycl_device_list] == 0} { + unsupported "target does not support SYCL" + return +} + +if {[build_executable "failed to compile $srcfile" "$binfile" "$srcfile" \ + {sycl debug}]} { + return +} + +foreach device $sycl_device_list { + if {![require_sycl_device "$device" "gpu" "Intel*"]} { + unsupported "test is aimed at Intel GPUs only" + continue + } + + sycl_with_intelgt_lock $device { + clean_restart ${testfile} + + if {![sycl_start $device]} { + continue + } + + # Set breakpoint inside the kernel. + set bp_location [gdb_get_line_number "inside-kernel"] + gdb_breakpoint "$srcfile:$bp_location" + + # Hit the breakpoint. + gdb_continue_to_breakpoint "kernel" ".*$srcfile:$bp_location.*" + + # Check if IGA is supposed to exist. + set has_iga 0 + gdb_test_multiple "show configuration" "check iga" { + -re -wrap "with-libiga64.*" { + set has_iga 1 + } + -re -wrap "without-libiga64.*" { + set has_iga 0 + } + } + + if {$has_iga} { + gdb_test "disassemble \$pc, \$pc+32" \ + [multi_line "Dump of assembler code from $hex to $hex:" \ + "=> $hex .*" \ + "End of assembler dump."] \ + "disassemble" + } else { + unsupported "disassemble" + + gdb_test "disassemble \$pc, \$pc+32" \ + [multi_line "Dump of assembler code from $hex to $hex:" \ + "=> $hex \[^\r\n\]+" \ + "Disassemble feature not available: libiga64 is missing." \ + "" \ + "unknown disassembler error.*"] \ + "disassembly is unavailable without iga" + } + } +} diff --git a/gdb/testsuite/gdb.arch/sycl-hello.cpp b/gdb/testsuite/gdb.arch/sycl-hello.cpp new file mode 100644 index 00000000000..3d2b8de407d --- /dev/null +++ b/gdb/testsuite/gdb.arch/sycl-hello.cpp @@ -0,0 +1,33 @@ +/* This testcase is part of GDB, the GNU debugger. + + Copyright 2026 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 . */ + +#include +#include "sycl-util.cpp" + +int +main (int argc, char *argv[]) +{ + sycl::queue queue {get_sycl_queue (argc, argv)}; + queue.single_task ([] () + { + int a = 0; /* inside-kernel */ + }); + + queue.wait (); + + return 0; +} -- 2.43.0 ________________________________________ Intel Deutschland GmbH Registered Address: Dornacher Strasse 1, 85622 Feldkirchen, Germany Tel: +49 (89) 99143-0 www.intel.de Managing Directors: Candice Moore, Jeffrey Schneiderman, Ramachandran Sitaraman Chairperson of the Supervisory Board: Sonja Pierer Registered Seat: Munich Commercial Register B: Amtsgericht Munich HRB 186928 This e-mail and any attachments may contain confidential material for the sole use of the intended recipient(s). Any review or distribution by others is strictly prohibited. If you are not the intended recipient, please contact the sender and delete all copies.