[PATCH v4 42/44] testsuite, arch, intelgt: add a disassembly test

From: Albertano Caruso <[email protected]>

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 <http://www.gnu.org/licenses/>.
+#
+# 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 <http://www.gnu.org/licenses/>.  */
+
+#include <sycl/sycl.hpp>
+#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.