User Guide
Installing and Using Red Hat Developer Toolset
Abstract
Making open source more inclusive
Red Hat is committed to replacing problematic language in our code, documentation, and web properties. We are beginning with these four terms: master, slave, blacklist, and whitelist. Because of the enormity of this endeavor, these changes will be implemented gradually over several upcoming releases. For more details, see our CTO Chris Wright’s message.
Part I. Introduction
Chapter 1. Red Hat Developer Toolset
1.1. About Red Hat Developer Toolset
Red Hat Developer Toolset is a Red Hat offering for developers on the Red Hat Enterprise Linux platform. It provides a complete set of development and performance analysis tools that can be installed and used on multiple versions of Red Hat Enterprise Linux. Executables built with the Red Hat Developer Toolset toolchain can then also be deployed and run on multiple versions of Red Hat Enterprise Linux. For detailed compatibility information, see Section 1.3, “Compatibility”.
Red Hat Developer Toolset does not replace the default system tools provided with Red Hat Enterprise Linux 7 when installed on those platforms. Instead, a parallel set of developer tools provides an alternative, newer version of those tools for optional use by developers. The default compiler and debugger, for example, remain those provided by the base Red Hat Enterprise Linux system.
What Is New in Red Hat Developer Toolset 12.1
Since Red Hat Developer Toolset 4.1, the Red Hat Developer Toolset content is also available in the ISO format together with the rest of Red Hat Software Collections content at https://access.redhat.com/downloads, specifically for Server and Workstation. Note that packages that require the Optional channel, which are discussed in Section 1.5.3, “Installing Optional Packages”, cannot be installed from the ISO image.
Name | Version | Description |
---|---|---|
GCC | 12.2.1 | A portable compiler suite with support for C, C++, and Fortran. |
binutils | 2.36.1 | A collection of binary tools and other utilities to inspect and manipulate object files and binaries. |
elfutils | 0.187 | A collection of binary tools and other utilities to inspect and manipulate ELF files. |
dwz | 0.14 | A tool to optimize DWARF debugging information contained in ELF shared libraries and ELF executables for size. |
GDB | 11.2 | A command line debugger for programs written in C, C++, and Fortran. |
ltrace | 0.7.91 | A debugging tool to display calls to dynamic libraries that a program makes. It can also monitor system calls executed by programs. |
strace | 5.18 | A debugging tool to monitor system calls that a program uses and signals it receives. |
memstomp | 0.1.5 | A debugging tool to identify calls to library functions with overlapping memory regions that are not allowed by various standards. |
SystemTap | 4.7 | A tracing and probing tool to monitor the activities of the entire system without the need to instrument, recompile, install, and reboot. |
Valgrind | 3.19.0 | An instrumentation framework and a number of tools to profile applications in order to detect memory errors, identify memory management problems, and report any use of improper arguments in system calls. |
OProfile | 1.4.0 | A system-wide profiler that uses the performance monitoring hardware on the processor to retrieve information about the kernel and executables on the system. |
Dyninst | 12.1.0 | A library for instrumenting and working with user-space executables during their execution. |
make | 4.3 | A dependency-tracking build automation tool. |
annobin | 11.08 | A build security checking tool. |
Red Hat Developer Toolset differs from "Technology Preview" compiler releases previously supplied in Red Hat Enterprise Linux in two important respects:
- Red Hat Developer Toolset can be used on multiple major and minor releases of Red Hat Enterprise Linux, as detailed in Section 1.3, “Compatibility”.
- Unlike Technology Preview compilers and other tools shipped in earlier Red Hat Enterprise Linux, Red Hat Developer Toolset is fully supported under Red Hat Enterprise Linux Subscription Level Agreements, is functionally complete, and is intended for production use.
Important bug fixes and security errata are issued to Red Hat Developer Toolset subscribers in a similar manner to Red Hat Enterprise Linux for two years from the release of each major version release. A new major version of Red Hat Developer Toolset is released annually, providing significant updates for existing components and adding major new components. A single minor release, issued six months after each new major version release, provides a smaller update of bug fixes, security errata, and new minor components.
Additionally, the Red Hat Enterprise Linux Application Compatibility Specification also applies to Red Hat Developer Toolset (subject to some constraints on the use of newer C++11 language features, detailed in Section 2.2.4, “C++ Compatibility”).
Applications and libraries provided by Red Hat Developer Toolset do not replace the Red Hat Enterprise Linux system versions, nor are they used in preference to the system versions. Using a framework called Software Collections, an additional set of developer tools is installed into the /opt/
directory and is explicitly enabled by the user on demand using the scl
utility.
1.2. Main Features
Red Hat Developer Toolset 12.1 brings the following changes:
- The Red Hat Developer Toolset version of the GNU Compiler Collection (GCC) has been upgraded to version 12.2.1 with many new features and bug fixes.
- The Red Hat Developer Toolset version of the GNU Debugger (GDB) has been upgraded to version 11.2 with many new features and bug fixes.
For a full list of changes and features introduced in this release, see Appendix B, Changes in Version 12.1.
1.3. Compatibility
Red Hat Developer Toolset 12.1 is available for Red Hat Enterprise Linux 7 for a number of architectures.
For ABI compatibility information, see Section 2.2.4, “C++ Compatibility”.
Runs on Red Hat Enterprise Linux 7.7 | Runs on Red Hat Enterprise Linux 7.9 | |
---|---|---|
Built with Red Hat Enterprise Linux 7.7 | Supported | Supported |
Built with Red Hat Enterprise Linux 7.9 | Not Supported | Supported |
Architecture support
Red Hat Developer Toolset is available on the following architectures:
- The 64-bit Intel and AMD architectures
- IBM Power Systems, big endian
- IBM Power Systems, little endian
- 64-bit IBM Z
1.4. Getting Access to Red Hat Developer Toolset
Red Hat Developer Toolset is an offering distributed as a part of Red Hat Software Collections.
This content set is available to customers with Red Hat Enterprise Linux 7 subscriptions listed at https://access.redhat.com/solutions/472793.
Enable Red Hat Developer Toolset by using Red Hat Subscription Management. For information on how to register your system with this subscription management service, see the Red Hat Subscription Management collection of guides.
1.4.1. Using Red Hat Software Collections
Complete the following steps to attach a subscription that provides access to the repository for Red Hat Software Collections (which includes Red Hat Developer Toolset), and then enable that repository:
Determine the pool ID of a subscription that provides Red Hat Software Collections (and thus also Red Hat Developer Toolset). To do so, display a list of all subscriptions that are available for your system:
# subscription-manager list --available
For each available subscription, this command displays its name, unique identifier, expiration date, and other details related to your subscription. The pool ID is listed on a line beginning with
Pool ID
.For a complete list of subscriptions that provide access to Red Hat Developer Toolset, see https://access.redhat.com/solutions/472793.
Attach the appropriate subscription to your system:
# subscription-manager attach --pool=pool_id
Replace pool_id with the pool ID you determined in the previous step. To verify the list of subscriptions your system has currently attached, at any time:
# subscription-manager list --consumed
Determine the exact name of the Red Hat Software Collections repository. Retrieve repository metadata and to display a list of available Yum repositories:
# subscription-manager repos --list
The repository names depend on the specific version of Red Hat Enterprise Linux you are using and are in the following format:
rhel-variant-rhscl-version-rpms rhel-variant-rhscl-version-debug-rpms rhel-variant-rhscl-version-source-rpms
In addition, certain packages, such as devtoolset-12-gcc-plugin-devel, depend on packages that are only available in the Optional channel. The repository names with these packages use the following format:
rhel-version-variant-optional-rpms rhel-version-variant-optional-debug-rpms rhel-version-variant-optional-source-rpms
For both the regular repositories and optional repositories, replace variant with the Red Hat Enterprise Linux system variant (
server
orworkstation
), and version with the Red Hat Enterprise Linux system version (7
).Enable the repositories from step no. 3:
# subscription-manager repos --enable repository
Replace repository with the name of the repository to enable.
Once the subscription is attached to the system, you can install Red Hat Developer Toolset as described in Section 1.5, “Installing Red Hat Developer Toolset”. For more information on how to register your system using Red Hat Subscription Management and associate it with subscriptions, see the Red Hat Subscription Management collection of guides.
1.5. Installing Red Hat Developer Toolset
Red Hat Developer Toolset is distributed as a collection of RPM packages that can be installed, updated, uninstalled, and inspected by using the standard package management tools that are included in Red Hat Enterprise Linux. Note that a valid subscription that provides access to the Red Hat Software Collections content set is required in order to install Red Hat Developer Toolset on your system. For detailed instructions on how to associate your system with an appropriate subscription and get access to Red Hat Developer Toolset, see Section 1.4, “Getting Access to Red Hat Developer Toolset”.
Before installing Red Hat Developer Toolset, install all available Red Hat Enterprise Linux updates.
1.5.1. Installing All Available Components
To install all components that are included in Red Hat Developer Toolset, install the devtoolset-12 package:
# yum install devtoolset-12
This installs all development, debugging, and performance monitoring tools, and other dependent packages to the system. Alternatively, you can choose to install only a selected package group as described in Section 1.5.2, “Installing Individual Package Groups”.
Note that since Red Hat Developer Toolset 3.0, the scl-utils package is not a part of Red Hat Developer Toolset, which is a change from preceding versions where the scl
utility was installed along with the Red Hat Developer Toolset software collection.
1.5.2. Installing Individual Package Groups
To make it easier to install only certain components, such as the integrated development environment or the software development toolchain, Red Hat Developer Toolset is distributed with a number of meta packages that allow you to install selected package groups as described in Table 1.3, “Red Hat Developer Toolset Meta Packages”.
Package Name | Description | Installed Components |
---|---|---|
devtoolset-12-perftools | Performance monitoring tools | SystemTap, Valgrind, OProfile, Dyninst |
devtoolset-12-toolchain | Development and debugging tools | GCC, make, GDB, binutils, elfutils, dwz, memstomp, strace, ltrace |
To install any of these meta packages:
# yum install package_name
Replace package_name with a space-separated list of meta packages you want to install. For example, to install only the development and debugging toolchain and packages that depend on it:
# yum install devtoolset-12-toolchain
Alternatively, you can choose to install all available components as described in Section 1.5.1, “Installing All Available Components”.
1.5.3. Installing Optional Packages
Red Hat Developer Toolset is distributed with a number of optional packages that are not installed by default. To list all Red Hat Developer Toolset packages that are available to you but not installed on your system:
$ yum list available devtoolset-12-\*
To install any of these optional packages:
# yum install package_name
Replace package_name with a space-separated list of packages that you want to install. For example, to install the devtoolset-12-gdb-gdbserver and devtoolset-12-gdb-doc packages:
# yum install devtoolset-12-gdb-gdbserver devtoolset-12-gdb-doc
1.5.4. Installing Debugging Information
To install debugging information for any of the Red Hat Developer Toolset packages, make sure that the yum-utils package is installed and run:
# debuginfo-install package_name
For example, to install debugging information for the devtoolset-12-dwz package:
# debuginfo-install devtoolset-12-dwz
Note that in order to use this command, you need to have access to the repository with these packages. If your system is registered with Red Hat Subscription Management, enable the rhel-variant-rhscl-version-debug-rpms
repository as described in Section 1.4, “Getting Access to Red Hat Developer Toolset”. For more information on how to get access to debuginfo packages, see https://access.redhat.com/site/solutions/9907.
The devtoolset-12-package_name-debuginfo packages can conflict with the corresponding packages from the base Red Hat Enterprise Linux system or from other versions of Red Hat Developer Toolset. This conflict also occurs in a multilib environment, where 64-bit debuginfo packages conflict with 32-bit debuginfo packages.
Manually uninstall the conflicting debuginfo packages prior to installing Red Hat Developer Toolset 12.1 and install only relevant debuginfo packages when necessary.
1.6. Updating Red Hat Developer Toolset
1.6.1. Updating to a Minor Version
When a new minor version of Red Hat Developer Toolset is available, update your Red Hat Enterprise Linux installation:
# yum update
This updates all packages on your Red Hat Enterprise Linux system, including the Red Hat Developer Toolset versions of development, debugging, and performance monitoring tools, and other dependent packages.
Use of Red Hat Developer Toolset requires the removal of any earlier pre-release versions of it. Additionally, it is not possible to update to Red Hat Developer Toolset 12.1 from a pre-release version of Red Hat Developer Toolset, including beta releases. If you have previously installed any pre-release version of Red Hat Developer Toolset, uninstall it from your system as described in Section 1.7, “Uninstalling Red Hat Developer Toolset” and install the new version as documented in Section 1.5, “Installing Red Hat Developer Toolset”.
1.6.2. Updating to a Major Version
When a new major version of Red Hat Developer Toolset is available, you can install it in parallel with the previous version. For detailed instructions on how to install Red Hat Developer Toolset on your system, see Section 1.5, “Installing Red Hat Developer Toolset”.
1.7. Uninstalling Red Hat Developer Toolset
To uninstall Red Hat Developer Toolset packages from your system:
# yum remove devtoolset-12\* libasan libatomic libcilkrts libitm liblsan libtsan libubsan
This removes the GNU Compiler Collection, GNU Debugger, binutils, and other packages that are a part of Red Hat Developer Toolset from the system.
Red Hat Developer Toolset 12.1 for Red Hat Enterprise Linux 7 no longer includes the libatomic
and libitm
libraries, which the above command attempts to remove, because they are not required for a proper function of Red Hat Developer Toolset components on that system. Nevertheless, the above command works as expected even on Red Hat Enterprise Linux 7.
Note that the uninstallation of the tools provided by Red Hat Developer Toolset does not affect the Red Hat Enterprise Linux system versions of these tools.
1.8. Using Red Hat Developer Toolset Container Images
Docker-formatted container images can be used to run Red Hat Developer Toolset components inside virtual software containers, thus isolating them from the host system and allowing for their rapid deployment. For detailed description of the Red Hat Developer Toolset docker-formatted container images and Red Hat Developer Toolset Dockerfiles, see Using Red Hat Software Collections Container Images.
The docker package, which contains the Docker daemon, command-line tool, and other necessary components for building and using docker-formatted container images, is currently available only for the Server variant of the Red Hat Enterprise Linux 7 product.
Follow the instructions outlined at Getting Docker in RHEL 7 to set up an environment for building and using docker-formatted container images.
1.9. Additional Resources
For more information about Red Hat Developer Toolset and Red Hat Enterprise Linux, see the resources listed below.
Online Documentation
- Red Hat Subscription Management collection of guides — The Red Hat Subscription Management collection of guides provides detailed information on how to manage subscriptions on Red Hat Enterprise Linux.
- Red Hat Developer Toolset 12.1 Release Notes — The Release Notes for Red Hat Developer Toolset 12.1 contain more information.
- Red Hat Enterprise Linux 7 Developer Guide — The Developer Guide for Red Hat Enterprise Linux 7 provides more information on the Eclipse IDE, libraries and runtime support, compiling and building, debugging, and profiling on these systems.
- Red Hat Enterprise Linux 7 Installation Guide — The Installation Guide for Red Hat Enterprise Linux 7 explains how to obtain, install, and update the system.
- Red Hat Enterprise Linux 7 System Administrator’s Guide — The System Administrator’s Guide for Red Hat Enterprise Linux 7 documents relevant information regarding the deployment, configuration, and administration of Red Hat Enterprise Linux 7.
- Using Red Hat Software Collections Container Images — This book provides information on how to use container images based on Red Hat Software Collections. The available container images include applications, daemons, databases, as well as the Red Hat Developer Toolset container images. The images can be run on Red Hat Enterprise Linux 7 Server and Red Hat Enterprise Linux Atomic Host.
- Getting Started with Containers — The guide contains a comprehensive overview of information about building and using container images on Red Hat Enterprise Linux 7 and Red Hat Enterprise Linux Atomic Host.
See Also
- Appendix B, Changes in Version 12.1 — A list of changes and improvements over the version of the Red Hat Developer Toolset tools in the previous version of Red Hat Developer Toolset.
Part II. Development Tools
Chapter 2. GNU Compiler Collection (GCC)
The GNU Compiler Collection, commonly abbreviated GCC, is a portable compiler suite with support for a wide selection of programming languages.
Red Hat Developer Toolset is distributed with GCC 12.2.1. This version is more recent than the version included in Red Hat Enterprise Linux and provides a number of bug fixes and enhancements.
2.1. GNU C Compiler
2.1.1. Installing the C Compiler
In Red Hat Developer Toolset, the GNU C compiler is provided by the devtoolset-12-gcc package and is automatically installed with devtoolset-12-toolchain as described in Section 1.5, “Installing Red Hat Developer Toolset”.
2.1.2. Using the C Compiler
To compile a C program on the command line, run the gcc
compiler as follows:
$ scl enable devtoolset-12 'gcc -o output_file source_file...'
This creates a binary file named output_file in the current working directory. If the -o
option is omitted, the compiler creates a file named a.out
by default.
When you are working on a project that consists of several source files, it is common to compile an object file for each of the source files first and then link these object files together. This way, when you change a single source file, you can recompile only this file without having to compile the entire project. To compile an object file on the command line,:
$ scl enable devtoolset-12 'gcc -o object_file -c source_file'
This creates an object file named object_file. If the -o
option is omitted, the compiler creates a file named after the source file with the .o
file extension. To link object files together and create a binary file:
$ scl enable devtoolset-12 'gcc -o output_file object_file...'
Note that you can execute any command using the scl
utility, causing it to be run with the Red Hat Developer Toolset binaries used in preference to the Red Hat Enterprise Linux system equivalent. This allows you to run a shell session with Red Hat Developer Toolset gcc
as default:
$ scl enable devtoolset-12 'bash'
To verify the version of gcc
you are using at any point:
$ which gcc
Red Hat Developer Toolset’s gcc
executable path will begin with /opt
. Alternatively, you can use the following command to confirm that the version number matches that for Red Hat Developer Toolset gcc
:
$ gcc -v
Example 2.1. Compiling a C Program on the Command Line
Consider a source file named hello.c
with the following contents:
#include <stdio.h> int main(int argc, char *argv[]) { printf("Hello, World!\n"); return 0; }
Compile this source code on the command line by using the gcc
compiler from Red Hat Developer Toolset:
$ scl enable devtoolset-12 'gcc -o hello hello.c'
This creates a new binary file called hello
in the current working directory.
2.1.3. Running a C Program
When gcc
compiles a program, it creates an executable binary file. To run this program on the command line, change to the directory with the executable file and run it:
$ ./file_name
Example 2.2. Running a C Program on the Command Line
Assuming that you have successfully compiled the hello
binary file as shown in Example 2.1, “Compiling a C Program on the Command Line”, you can run it by typing the following at a shell prompt:
$ ./hello
Hello, World!
2.2. GNU C++ Compiler
2.2.1. Installing the C++ Compiler
In Red Hat Developer Toolset, the GNU C++ compiler is provided by the devtoolset-12-gcc-c++ package and is automatically installed with the devtoolset-12-toolchain package as described in Section 1.5, “Installing Red Hat Developer Toolset”.
2.2.2. Using the C++ Compiler
To compile a C++ program on the command line, run the g++
compiler as follows:
$ scl enable devtoolset-12 'g++ -o output_file source_file...'
This creates a binary file named output_file in the current working directory. If the -o
option is omitted, the g++
compiler creates a file named a.out
by default.
When you are working on a project that consists of several source files, it is common to compile an object file for each of the source files first and then link these object files together. This way, when you change a single source file, you can recompile only this file without having to compile the entire project. To compile an object file on the command line:
$ scl enable devtoolset-12 'g++ -o object_file -c source_file'
This creates an object file named object_file. If the -o
option is omitted, the g++
compiler creates a file named after the source file with the .o
file extension. To link object files together and create a binary file:
$ scl enable devtoolset-12 'g++ -o output_file object_file...'
Note that you can execute any command using the scl
utility, causing it to be run with the Red Hat Developer Toolset binaries used in preference to the Red Hat Enterprise Linux system equivalent. This allows you to run a shell session with Red Hat Developer Toolset g++
as default:
$ scl enable devtoolset-12 'bash'
To verify the version of g++
you are using at any point:
$ which g++
Red Hat Developer Toolset’s g++
executable path will begin with /opt. Alternatively, you can use the following command to confirm that the version number matches that for Red Hat Developer Toolset g++
:
$ g++ -v
Example 2.3. Compiling a C++ Program on the Command Line
Consider a source file named hello.cpp
with the following contents:
#include <iostream> using namespace std; int main(int argc, char *argv[]) { cout << "Hello, World!" << endl; return 0; }
Compile this source code on the command line by using the g++
compiler from Red Hat Developer Toolset:
$ scl enable devtoolset-12 'g++ -o hello hello.cpp'
This creates a new binary file called hello
in the current working directory.
2.2.3. Running a C++ Program
When g++
compiles a program, it creates an executable binary file. To run this program on the command line, change to the directory with the executable file and run it:
$ ./file_name
Example 2.4. Running a C++ Program on the Command Line
Assuming that you have successfully compiled the hello
binary file as shown in Example 2.3, “Compiling a C++ Program on the Command Line”, you can run it:
$ ./hello
Hello, World!
2.2.4. C++ Compatibility
All compilers from Red Hat Enterprise Linux versions 5, 6, and 7 and from Red Hat Developer Toolset versions 1 to 10 in any -std
mode are compatible with any other of those compilers in C++98 mode.
A compiler in C++11, C++14, or C++17 mode is only guaranteed to be compatible with another compiler in those same modes if they are from the same release series.
Supported examples:
- C++11 and C++11 from Red Hat Developer Toolset 6.x
- C++14 and C++14 from Red Hat Developer Toolset 6.x
- C++17 and C++17 from Red Hat Developer Toolset 10.x
- The GCC compiler in Red Hat Developer Toolset 10.x can build code using C++20 but this capability is experimental and not supported by Red Hat.
- All compatibility information mentioned in this section is relevant only for Red Hat-supplied versions of the GCC C++ compiler.
2.2.4.1. C++ ABI
Any C++98-compliant binaries or libraries built by the Red Hat Developer Toolset toolchain explicitly with -std=c++98
or -std=gnu++98
can be freely mixed with binaries and shared libraries built by the Red Hat Enterprise Linux 5, 6 or 7 system GCC.
The default language standard setting for Red Hat Developer Toolset 12.1 is C++17 with GNU extensions, equivalent to explicitly using option -std=gnu++17
.
Using the C++14 language version is supported in Red Hat Developer Toolset when all C++ objects compiled with the respective flag have been built using Red Hat Developer Toolset 6 or later. Objects compiled by the system GCC in its default mode of C++98 are also compatible, but objects compiled with the system GCC in C++11 or C++14 mode are not compatible.
Starting with Red Hat Developer Toolset 10.x, using the C++17 language version is no longer experimental and is supported by Red Hat. All C++ objects compiled with C++17 must be built using Red Hat Developer Toolset 10.x or later.
Use of C++11, C++14, and C++17 features in your application requires careful consideration of the above ABI compatibility information.
The mixing of objects, binaries and libraries, built by the Red Hat Enterprise Linux 7 system toolchain GCC using the -std=c++0x
or -std=gnu++0x
flags, with those built with the C++11 or later language versions using the GCC in Red Hat Developer Toolset is explicitly not supported.
Aside from the C++11, C++14, and C++17 ABI, discussed above, the Red Hat Enterprise Linux Application Compatibility Specification is unchanged for Red Hat Developer Toolset. When mixing objects built with Red Hat Developer Toolset with those built with the Red Hat Enterprise Linux 7 toolchain (particularly .o
/.a
files), the Red Hat Developer Toolset toolchain should be used for any linkage. This ensures any newer library features provided only by Red Hat Developer Toolset are resolved at link-time.
A new standard mangling for SIMD vector types has been added to avoid name clashes on systems with vectors of varying lengths. The compiler in Red Hat Developer Toolset uses the new mangling by default. It is possible to use the previous standard mangling by adding the -fabi-version=2
or -fabi-version=3
options to GCC C++ compiler calls. To display a warning about code that uses the old mangling, use the -Wabi
option.
On Red Hat Enterprise Linux 7, the GCC C++ compiler still uses the old mangling by default, but emits aliases with the new mangling on targets that support strong aliases. It is possible to use the new standard mangling by adding the -fabi-version=4
option to compiler calls. To display a warning about code that uses the old mangling, use the -Wabi
option.
2.3. GNU Fortran Compiler
2.3.1. Installing the Fortran Compiler
In Red Hat Developer Toolset, the GNU Fortran compiler is provided by the devtoolset-12-gcc-gfortran package and is automatically installed with devtoolset-12-toolchain as described in Section 1.5, “Installing Red Hat Developer Toolset”.
2.3.2. Using the Fortran Compiler
To compile a Fortran program on the command line, run the gfortran
compiler as follows:
$ scl enable devtoolset-12 'gfortran -o output_file source_file...'
This creates a binary file named output_file in the current working directory. If the -o
option is omitted, the compiler creates a file named a.out
by default.
When you are working on a project that consists of several source files, it is common to compile an object file for each of the source files first and then link these object files together. This way, when you change a single source file, you can recompile only this file without having to compile the entire project. To compile an object file on the command line:
$ scl enable devtoolset-12 'gfortran -o object_file -c source_file'
This creates an object file named object_file. If the -o
option is omitted, the compiler creates a file named after the source file with the .o
file extension. To link object files together and create a binary file:
$ scl enable devtoolset-12 'gfortran -o output_file object_file...'
Note that you can execute any command using the scl
utility, causing it to be run with the Red Hat Developer Toolset binaries used in preference to the Red Hat Enterprise Linux system equivalent. This allows you to run a shell session with Red Hat Developer Toolset gfortran
as default:
$ scl enable devtoolset-12 'bash'
To verify the version of gfortran
you are using at any point:
$ which gfortran
Red Hat Developer Toolset’s gfortran
executable path will begin with /opt
. Alternatively, you can use the following command to confirm that the version number matches that for Red Hat Developer Toolset gfortran
:
$ gfortran -v
Example 2.5. Compiling a Fortran Program on the Command Line
Consider a source file named hello.f
with the following contents:
program hello print *, "Hello, World!" end program hello
Compile this source code on the command line by using the gfortran
compiler from Red Hat Developer Toolset:
$ scl enable devtoolset-12 'gfortran -o hello hello.f'
This creates a new binary file called hello
in the current working directory.
2.3.3. Running a Fortran Program
When gfortran
compiles a program, it creates an executable binary file. To run this program on the command line, change to the directory with the executable file and run it:
$ ./file_name
Example 2.6. Running a Fortran Program on the Command Line
Assuming that you have successfully compiled the hello
binary file as shown in Example 2.5, “Compiling a Fortran Program on the Command Line”, you can run it:
$ ./hello
Hello, World!
2.4. Specifics of GCC in Red Hat Developer Toolset
Static linking of libraries
Certain more recent library features are statically linked into applications built with Red Hat Developer Toolset to support execution on multiple versions of Red Hat Enterprise Linux. This creates an additional minor security risk as standard Red Hat Enterprise Linux errata do not change this code. If the need arises for developers to rebuild their applications due to this risk, Red Hat will communicate this using a security erratum.
Because of this additional security risk, developers are strongly advised not to statically link their entire application for the same reasons.
Specify libraries after object files when linking
In Red Hat Developer Toolset, libraries are linked using linker scripts which might specify some symbols through static archives. This is required to ensure compatibility with multiple versions of Red Hat Enterprise Linux. However, the linker scripts use the names of the respective shared object files. As a consequence, the linker uses different symbol handling rules than expected, and does not recognize symbols required by object files when the option adding the library is specified before options specifying the object files:
$ scl enable devtoolset-12 'gcc -lsomelib objfile.o'
Using a library from the Red Hat Developer Toolset in this manner results in the linker error message undefined reference to symbol
. To prevent this problem, follow the standard linking practice, and specify the option adding the library after the options specifying the object files:
$ scl enable devtoolset-12 'gcc objfile.o -lsomelib'
Note that this recommendation also applies when using the base Red Hat Enterprise Linux version of GCC.
2.5. Additional Resources
For more information about the GNU Compiler Collections and its features, see the resources listed below.
Installed Documentation
gcc(1) — The manual page for the
gcc
compiler provides detailed information on its usage; with few exceptions,g++
accepts the same command line options asgcc
. To display the manual page for the version included in Red Hat Developer Toolset:$
scl enable devtoolset-12 'man gcc'
gfortran(1) — The manual page for the
gfortran
compiler provides detailed information on its usage. To display the manual page for the version included in Red Hat Developer Toolset:$
scl enable devtoolset-12 'man gfortran'
C++ Standard Library Documentation — Documentation on the C++ standard library can be optionally installed:
# yum install devtoolset-12-libstdc++-docs
Once installed, HTML documentation is available at
/opt/rh/devtoolset-12/root/usr/share/doc/devtoolset-12-libstdC++-docs-12.2.1/html/index.html
.
Online Documentation
- Red Hat Enterprise Linux 7 Developer Guide — The Developer Guide for Red Hat Enterprise Linux 7 provides in-depth information about GCC.
- Using the GNU Compiler Collection — The upstream GCC manual provides an in-depth description of the GNU compilers and their usage.
- The GNU C++ Library — The GNU C++ library documentation provides detailed information about the GNU implementation of the standard C++ library.
-
The GNU Fortran Compiler — The GNU Fortran compiler documentation provides detailed information on
gfortran
's usage.
See Also
- Chapter 1, Red Hat Developer Toolset — An overview of Red Hat Developer Toolset and more information on how to install it on your system.
- Chapter 4, binutils — Instructions on using binutils, a collection of binary tools to inspect and manipulate object files and binaries.
- Chapter 5, elfutils — Instructions on using elfutils, a collection of binary tools to inspect and manipulate ELF files.
- Chapter 6, dwz — Instructions on using the dwz tool to optimize DWARF debugging information contained in ELF shared libraries and ELF executables for size.
- Chapter 8, GNU Debugger (GDB) — Instructions on debugging programs written in C, C++, and Fortran.
Chapter 3. GNU make
The GNU make utility, commonly abbreviated make, is a tool for controlling the generation of executables from source files. make automatically determines which parts of a complex program have changed and need to be recompiled. make uses configuration files called Makefiles to control the way programs are built.
Red Hat Developer Toolset is distributed with make 4.3. This version is more recent than the version included in Red Hat Enterprise Linux and provides a number of bug fixes and enhancements.
3.1. Installing make
In Red Hat Developer Toolset, GNU make is provided by the devtoolset-12-make package and is automatically installed with devtoolset-12-toolchain as described in Section 1.5, “Installing Red Hat Developer Toolset”.
3.2. Using make
To build a program without using a Makefile, run the make
tool as follows:
$ scl enable devtoolset-12 'make source_file_without_extension'
This command makes use of implicit rules that are defined for a number of programming languages, including C, C++, and Fortran. The result is a binary file named source_file_without_extension in the current working directory.
Note that you can execute any command using the scl
utility, causing it to be run with the Red Hat Developer Toolset binaries used in preference to the Red Hat Enterprise Linux system equivalent. This allows you to run a shell session with Red Hat Developer Toolset make
as default:
$ scl enable devtoolset-12 'bash'
To verify the version of make
you are using at any point:
$ which make
Red Hat Developer Toolset’s make
executable path will begin with /opt
. Alternatively, you can use the following command to confirm that the version number matches that for Red Hat Developer Toolset make
:
$ make -v
Example 3.1. Building a C Program Using make
Consider a source file named hello.c
with the following contents:
#include <stdio.h> int main(int argc, char *argv[]) { printf("Hello, World!\n"); return 0; }
Build this source code using the implicit rules defined by the make
utility from Red Hat Developer Toolset:
$ scl enable devtoolset-12 'make hello'
cc hello.c -o hello
This creates a new binary file called hello
in the current working directory.
3.3. Using Makefiles
To build complex programs that consist of a number of source files, make uses configuration files called Makefiles that control how to compile the components of a program and build the final executable. Makefiles can also contain instructions for cleaning the working directory, installing and uninstalling program files, and other operations.
make automatically uses files named GNUmakefile
, makefile
, or Makefile
in the current directory. To specify another file name, use the -f
option:
$ make -f make_file
Describing the details of Makefile syntax is beyond the scope of this guide. See GNU make, the upstream GNU make manual, which provides an in-depth description of the GNU make utility, Makefile syntax, and their usage.
The full make manual is also available in the Texinfo format as a part of your installation. To view this manual:
$ scl enable devtoolset-12 'info make'
Example 3.2. Building a C Program Using a Makefile
Consider the following universal Makefile named Makefile
for building the simple C program introduced in Example 3.1, “Building a C Program Using make”. The Makefile defines some variables and specifies four rules, which consist of targets and their recipes. Note that the lines with recipes must start with the TAB character:
CC=gcc CFLAGS=-c -Wall SOURCE=hello.c OBJ=$(SOURCE:.c=.o) EXE=hello all: $(SOURCE) $(EXE) $(EXE): $(OBJ) $(CC) $(OBJ) -o $@ .o: .c $(CC) $(CFLAGS) $< -o $@ clean: rm -rf $(OBJ) $(EXE)
To build the hello.c
program using this Makefile, run the make
utility:
$ scl enable devtoolset-12 'make'
gcc -c -Wall hello.c -o hello.o
gcc hello.o -o hello
This creates a new object file hello.o
and a new binary file called hello
in the current working directory.
To clean the working directory, run:
$ scl enable devtoolset-12 'make clean'
rm -rf hello.o hello
This removes the object and binary files from the working directory.
3.4. Additional Resources
For more information about the GNU make tool and its features, see the resources listed below.
Installed Documentation
make(1) — The manual page for the
make
utility provides information on its usage. To display the manual page for the version included in Red Hat Developer Toolset:$
scl enable devtoolset-12 'man make'
The full make manual, which includes detailed information about Makefile syntax, is also available in the Texinfo format. To display the info manual for the version included in Red Hat Developer Toolset:
$
scl enable devtoolset-12 'info make'
Online Documentation
- GNU make — The upstream GNU make manual provides an in-depth description of the GNU make utility, Makefile syntax, and their usage.
See Also
- Chapter 1, Red Hat Developer Toolset — An overview of Red Hat Developer Toolset and more information on how to install it on your system.
- Chapter 2, GNU Compiler Collection (GCC) — Instructions on using the GNU Compiler Collection, a portable compiler suite with support for a wide selection of programming languages.
- Chapter 4, binutils — Instructions on using binutils, a collection of binary tools to inspect and manipulate object files and binaries.
- Chapter 5, elfutils — Instructions on using elfutils, a collection of binary tools to inspect and manipulate ELF files.
- Chapter 6, dwz — Instructions on using the dwz tool to optimize DWARF debugging information contained in ELF shared libraries and ELF executables for size.
- Chapter 8, GNU Debugger (GDB) — Instructions on debugging programs written in C, C++, and Fortran.
Chapter 4. binutils
binutils is a collection of various binary tools, such as the GNU linker, GNU assembler, and other utilities that allow you to inspect and manipulate object files and binaries. See Table 4.1, “Tools Included in binutils for Red Hat Developer Toolset” for a complete list of binary tools that are distributed with the Red Hat Developer Toolset version of binutils.
Red Hat Developer Toolset is distributed with binutils 2.36.1. This version is more recent than the version included in Red Hat Enterprise Linux and the previous release of Red Hat Developer Toolset and provides bug fixes and enhancements.
Name | Description |
---|---|
| Translates addresses into file names and line numbers. |
| Creates, modifies, and extracts files from archives. |
| The GNU assembler. |
| Decodes mangled C++ symbols. |
| Combines DWARF object files into a single DWARF package file. |
| Examines and edits ELF files. |
| Display profiling information. |
| The GNU linker. |
| An alternative to the GNU linker. |
| Another alternative to the GNU linker. |
| Lists symbols from object files. |
| Copies and translates object files. |
| Displays information from object files. |
| Generates an index to the contents of an archive to make access to this archive faster. |
| Displays information about ELF files. |
| Lists section sizes of object or archive files. |
| Displays printable character sequences in files. |
| Discards all symbols from object files. |
4.1. Installing binutils
In Red Hat Developer Toolset, binutils are provided by the devtoolset-12-binutils package and are automatically installed with devtoolset-12-toolchain as described in Section 1.5, “Installing Red Hat Developer Toolset”.
4.2. Using the GNU Assembler
To produce an object file from an assembly language program, run the as
tool as follows:
$ scl enable devtoolset-12 'as option ... -o object_file source_file'
This creates an object file named object_file in the current working directory.
Note that you can execute any command using the scl
utility, causing it to be run with the Red Hat Developer Toolset binaries used in preference to the Red Hat Enterprise Linux system equivalent. This allows you to run a shell session with Red Hat Developer Toolset as
as default:
$ scl enable devtoolset-12 'bash'
To verify the version of as
you are using at any point:
$ which as
Red Hat Developer Toolset’s as
executable path will begin with /opt
. Alternatively, you can use the following command to confirm that the version number matches that for Red Hat Developer Toolset as
:
$ as -v
4.3. Using the GNU Linker
To create an executable binary file or a library from object files, run the ld
tool as follows:
$ scl enable devtoolset-12 'ld option ... -o output_file object_file ...'
This creates a binary file named output_file in the current working directory. If the -o
option is omitted, the compiler creates a file named a.out
by default.
Note that you can execute any command using the scl
utility, causing it to be run with the Red Hat Developer Toolset binaries used in preference to the Red Hat Enterprise Linux system equivalent. This allows you to run a shell session with Red Hat Developer Toolset ld
as default:
$ scl enable devtoolset-12 'bash'
To verify the version of ld
you are using at any point:
$ which ld
Red Hat Developer Toolset’s ld
executable path will begin with /opt
. Alternatively, you can use the following command to confirm that the version number matches that for Red Hat Developer Toolset ld
:
$ ld -v
4.4. Using Other Binary Tools
The binutils provide many binary tools other than a linker and an assembler. For a complete list of these tools, see Table 4.1, “Tools Included in binutils for Red Hat Developer Toolset”.
To execute any of the tools that are a part of binutils:
$ scl enable devtoolset-12 'tool option ... file_name'
See Table 4.1, “Tools Included in binutils for Red Hat Developer Toolset” for a list of tools that are distributed with binutils. For example, to use the objdump
tool to inspect an object file:
$ scl enable devtoolset-12 'objdump option ... object_file'
Note that you can execute any command using the scl
utility, causing it to be run with the Red Hat Developer Toolset binaries used in preference to the Red Hat Enterprise Linux system equivalent. This allows you to run a shell session with Red Hat Developer Toolset binary tools as default:
$ scl enable devtoolset-12 'bash'
To verify the version of binutils you are using at any point:
$ which objdump
Red Hat Developer Toolset’s objdump
executable path will begin with /opt
. Alternatively, you can use the following command to confirm that the version number matches that for Red Hat Developer Toolset objdump
:
$ objdump -v
4.5. Specifics of binutils in Red Hat Developer Toolset
Static linking of libraries
Certain more recent library features are statically linked into applications built with Red Hat Developer Toolset to support execution on multiple versions of Red Hat Enterprise Linux. This creates an additional minor security risk as standard Red Hat Enterprise Linux errata do not change this code. If the need arises for developers to rebuild their applications due to this risk, Red Hat will communicate this using a security erratum.
Because of this additional security risk, developers are strongly advised not to statically link their entire application for the same reasons.
Specify libraries after object files when linking
In Red Hat Developer Toolset, libraries are linked using linker scripts which might specify some symbols through static archives. This is required to ensure compatibility with multiple versions of Red Hat Enterprise Linux. However, the linker scripts use the names of the respective shared object files. As a consequence, the linker uses different symbol handling rules than expected, and does not recognize symbols required by object files when the option adding the library is specified before options specifying the object files:
$ scl enable devtoolset-12 'ld -lsomelib objfile.o'
Using a library from the Red Hat Developer Toolset in this manner results in the linker error message undefined reference to symbol
. To prevent this problem, follow the standard linking practice, and specify the option adding the library after the options specifying the object files:
$ scl enable devtoolset-12 'ld objfile.o -lsomelib'
Note that this recommendation also applies when using the base Red Hat Enterprise Linux version of binutils.
4.6. Additional Resources
For more information about binutils, see the resources listed below.
Installed Documentation
as(1), ld(1), addr2line(1), ar(1), c++filt(1), dwp(1), elfedit(1), gprof(1), nm(1), objcopy(1), objdump(1), ranlib(1), readelf(1), size(1), strings(1), strip(1), — Manual pages for various binutils tools provide more information about their respective usage. To display a manual page for the version included in Red Hat Developer Toolset:
$
scl enable devtoolset-12 'man tool'
Online Documentation
- Documentation for binutils — The binutils documentation provides an in-depth description of the binary tools and their usage.
See Also
- Chapter 1, Red Hat Developer Toolset — An overview of Red Hat Developer Toolset and more information on how to install it on your system.
- Chapter 5, elfutils — Information on how to use elfutils, a collection of binary tools to inspect and manipulate ELF files.
- Chapter 2, GNU Compiler Collection (GCC) — Information on how to compile programs written in C, C++, and Fortran.
Chapter 5. elfutils
elfutils is a collection of various binary tools, such as eu-objdump
, eu-readelf
, and other utilities that allow you to inspect and manipulate ELF files. See Table 5.1, “Tools Included in elfutils for Red Hat Developer Toolset” for a complete list of binary tools that are distributed with the Red Hat Developer Toolset version of elfutils.
Red Hat Developer Toolset is distributed with elfutils 0.187. This version is more recent than the version included the previous release of Red Hat Developer Toolset and provides some bug fixes and enhancements.
Name | Description |
---|---|
| Translates addresses into file names and line numbers. |
| Creates, modifies, and extracts files from archives. |
| Compares relevant parts of two ELF files for equality. |
| Verifies that ELF files are compliant with the generic ABI (gABI) and processor-specific supplement ABI (psABI) specification. |
| Locates the source of text relocations in files. |
| Creates an offline archive for debugging. |
| Lists symbols from object files. |
| Displays information from object files. |
| Generates an index to the contents of an archive to make access to this archive faster. |
| Displays information about ELF files. |
| Lists section sizes of object or archive files. |
| A new utility for unwinding processes and cores. |
| Displays printable character sequences in files. |
| Discards all symbols from object files. |
| Combines stripped files with separate symbols and debug information. |
5.1. Installing elfutils
In Red Hat Developer Toolset, elfutils is provided by the devtoolset-12-elfutils package and is automatically installed with devtoolset-12-toolchain as described in Section 1.5, “Installing Red Hat Developer Toolset”.
5.2. Using elfutils
To execute any of the tools that are part of elfutils, run the tool as follows:
$ scl enable devtoolset-12 'tool option ... file_name'
See Table 5.1, “Tools Included in elfutils for Red Hat Developer Toolset” for a list of tools that are distributed with elfutils. For example, to use the eu-objdump
tool to inspect an object file:
$ scl enable devtoolset-12 'eu-objdump option ... object_file'
Note that you can execute any command using the scl
utility, causing it to be run with the Red Hat Developer Toolset binaries used in preference to the Red Hat Enterprise Linux system equivalent. This allows you to run a shell session with Red Hat Developer Toolset binary tools as default:
$ scl enable devtoolset-12 'bash'
To verify the version of elfutils you are using at any point:
$ which eu-objdump
Red Hat Developer Toolset’s eu-objdump
executable path will begin with /opt
. Alternatively, you can use the following command to confirm that the version number matches that for Red Hat Developer Toolset eu-objdump
:
$ eu-objdump -V
5.3. Additional Resources
For more information about elfutils, see the resources listed below.
See Also
- Chapter 1, Red Hat Developer Toolset — An overview of Red Hat Developer Toolset and more information on how to install it on your system.
- Chapter 2, GNU Compiler Collection (GCC) — Instructions on compiling programs written in C, C++, and Fortran.
- Chapter 4, binutils — Instructions on using binutils, a collection of binary tools to inspect and manipulate object files and binaries.
- Chapter 6, dwz — Instructions on using the dwz tool to optimize DWARF debugging information contained in ELF shared libraries and ELF executables for size.
Chapter 6. dwz
dwz is a command line tool that attempts to optimize DWARF debugging information contained in ELF shared libraries and ELF executables for size. To do so, dwz
replaces DWARF information representation with equivalent smaller representation where possible and reduces the amount of duplication by using techniques from Appendix E of the DWARF Standard.
Red Hat Developer Toolset is distributed with dwz 0.14.
6.1. Installing dwz
In Red Hat Developer Toolset, the dwz
utility is provided by the devtoolset-12-dwz package and is automatically installed with devtoolset-12-toolchain as described in Section 1.5, “Installing Red Hat Developer Toolset”.
6.2. Using dwz
To optimize DWARF debugging information in a binary file, run the dwz
tool as follows:
$ scl enable devtoolset-12 'dwz option... file_name'
Note that you can execute any command using the scl
utility, causing it to be run with the Red Hat Developer Toolset binaries used in preference to the Red Hat Enterprise Linux system equivalent. This allows you to run a shell session with Red Hat Developer Toolset dwz
as default:
$ scl enable devtoolset-12 'bash'
To verify the version of dwz
you are using at any point:
$ which dwz
Red Hat Developer Toolset’s dwz
executable path will begin with /opt
. Alternatively, you can use the following command to confirm that the version number matches that for Red Hat Developer Toolset dwz
:
$ dwz -v
6.3. Additional Resources
For more information about dwz and its features, see the resources listed below.
Installed Documentation
dwz(1) — The manual page for the
dwz
utility provides detailed information on its usage. To display the manual page for the version included in Red Hat Developer Toolset:$
scl enable devtoolset-12 'man dwz'
See Also
- Chapter 1, Red Hat Developer Toolset — An overview of Red Hat Developer Toolset and more information on how to install it on your system.
- Chapter 2, GNU Compiler Collection (GCC) — Instructions on compiling programs written in C, C++, and Fortran.
- Chapter 4, binutils — Instructions on using binutils, a collection of binary tools to inspect and manipulate object files and binaries.
- Chapter 5, elfutils — Instructions on using elfutils, a collection of binary tools to inspect and manipulate ELF files.
Chapter 7. Annobin
The Annobin project consists of the annobin
plugin and the annockeck
program.
The annobin
plugin scans the GNU Compiler Collection (GCC) command line, the compilation state, and the compilation process, and generates the ELF notes. The ELF notes record how the binary was built and provide information for the annocheck
program to perform security hardening checks.
The security hardening checker is part of the annocheck
program and is enabled by default. It checks the binary files to determine whether the program was built with necessary security hardening options and compiled correctly. annocheck
is able to recursively scan directories, archives, and RPM packages for ELF object files.
The files must be in ELF format. annocheck
does not handle any other binary file types.
7.1. Installing Annobin
In Red Hat Developer Toolset, the annobin
plugin and the annockeck
program are provided by the devtoolset-12-gcc package and are installed as described in Section 1.5.3, “Installing Optional Packages”.
7.2. Using Annobin Plugin
To pass options to the annobin
plugin with gcc
, use:
$ scl enable devtoolset-12 'gcc -fplugin=annobin -fplugin-arg-annobin-option file-name'
Note that you can execute any command using the scl
utility, causing it to be run with the Red Hat Developer Toolset binaries used in preference to the Red Hat Enterprise Linux system equivalent. This allows you to run a shell session with Red Hat Developer Toolset as
as default:
$ scl enable devtoolset-12 'bash'
7.3. Using Annocheck
To scan files, directories or RPM packages with the annocheck
program:
$ scl enable devtoolset-12 'annocheck file-name'
annocheck
only looks for the ELF files. Other file types are ignored.
Note that you can execute any command using the scl
utility, causing it to be run with the Red Hat Developer Toolset binaries used in preference to the Red Hat Enterprise Linux system equivalent. This allows you to run a shell session with Red Hat Developer Toolset as
as default:
$ scl enable devtoolset-12 'bash'
To verify the version of annocheck
you are using at any point:
$ which annocheck
Red Hat Developer Toolset’s annocheck
executable path will begin with /opt
. Alternatively, you can use the following command to confirm that the version number matches that for Red Hat Developer Toolset annocheck
:
$ annocheck --version
7.4. Additional Resources
For more information about annocheck, annobin and its features, see the resources listed below.
Installed Documentation
annocheck(1) — The manual page for the
annocheck
utility provides detailed information on its usage. To display the manual page for the version included in Red Hat Developer Toolset:$ scl enable devtoolset-12 'man annocheck'
annobin(1) — The manual page for the
annobin
utility provides detailed information on its usage. To display the manual page for the version included in Red Hat Developer Toolset:$ scl enable devtoolset-12 'man annobin'
Part III. Debugging Tools
Chapter 8. GNU Debugger (GDB)
The GNU Debugger, commonly abbreviated as GDB, is a command line tool that can be used to debug programs written in various programming languages. It allows you to inspect memory within the code being debugged, control the execution state of the code, detect the execution of particular sections of code, and much more.
Red Hat Developer Toolset is distributed with GDB 11.2. This version is more recent than the version included in Red Hat Enterprise Linux and the previous release of Red Hat Developer Toolset and provides some enhancements and numerous bug fixes.
8.1. Installing the GNU Debugger
In Red Hat Developer Toolset, the GNU Debugger is provided by the devtoolset-12-gdb package and is automatically installed with devtoolset-12-toolchain as described in Section 1.5, “Installing Red Hat Developer Toolset”.
8.2. Preparing a Program for Debugging
Compiling Programs with Debugging Information
To compile a C program with debugging information that can be read by the GNU Debugger, make sure the gcc
compiler is run with the -g
option:
$ scl enable devtoolset-12 'gcc -g -o output_file input_file...'
Similarly, to compile a C++ program with debugging information:
$ scl enable devtoolset-12 'g++ -g -o output_file input_file...'
Example 8.1. Compiling a C Program With Debugging Information
Consider a source file named fibonacci.c
that has the following contents:
#include <stdio.h> #include <limits.h> int main (int argc, char *argv[]) { unsigned long int a = 0; unsigned long int b = 1; unsigned long int sum; while (b < LONG_MAX) { printf("%ld ", b); sum = a + b; a = b; b = sum; } return 0; }
Compile this program on the command line using GCC from Red Hat Developer Toolset with debugging information for the GNU Debugger:
$ scl enable devtoolset-12 'gcc -g -o fibonacci fibonacci.c'
This creates a new binary file called fibonacci
in the current working directory.
Installing Debugging Information for Existing Packages
To install debugging information for a package that is already installed on the system:
# debuginfo-install package_name
Note that the yum-utils package must be installed for the debuginfo-install
utility to be available on your system.
Example 8.2. Installing Debugging Information for the glibc Package
Install debugging information for the glibc package:
# debuginfo-install glibc
Loaded plugins: product-id, refresh-packagekit, subscription-manager
--> Running transaction check
---> Package glibc-debuginfo.x86_64 0:2.17-105.el7 will be installed
...
8.3. Running the GNU Debugger
To run the GNU Debugger on a program you want to debug:
$ scl enable devtoolset-12 'gdb file_name'
This starts the gdb
debugger in interactive mode and displays the default prompt, (gdb)
. To quit the debugging session and return to the shell prompt, run the following command at any time:
(gdb) quit
Note that you can execute any command using the scl
utility, causing it to be run with the Red Hat Developer Toolset binaries used in preference to the Red Hat Enterprise Linux system equivalent. This allows you to run a shell session with Red Hat Developer Toolset gdb
as default:
$ scl enable devtoolset-12 'bash'
To verify the version of gdb
you are using at any point:
$ which gdb
Red Hat Developer Toolset’s gdb
executable path will begin with /opt
. Alternatively, you can use the following command to confirm that the version number matches that for Red Hat Developer Toolset gdb
:
$ gdb -v
Example 8.3. Running the gdb Utility on the fibonacci Binary File
This example assumes that you have successfully compiled the fibonacci
binary file as shown in Example 8.1, “Compiling a C Program With Debugging Information”.
Start debugging fibonacci
with gdb
:
$ scl enable devtoolset-12 'gdb fibonacci' GNU gdb (GDB) Red Hat Enterprise Linux 8.2-2.el7 Copyright (C) 2017 Free Software Foundation, Inc. License GPLv3+: GNU GPL version 3 or later <http://gnu.org/licenses/gpl.html> This is free software: you are free to change and redistribute it. There is NO WARRANTY, to the extent permitted by law. Type "show copying" and "show warranty" for details. This GDB was configured as "x86_64-redhat-linux-gnu". Type "show configuration" for configuration details. For bug reporting instructions, please see: <http://www.gnu.org/software/gdb/bugs/>. Find the GDB manual and other documentation resources online at: <http://www.gnu.org/software/gdb/documentation/>. For help, type "help". Type "apropos word" to search for commands related to "word"... Reading symbols from fibonacci...done. (gdb)
8.4. Listing Source Code
To view the source code of the program you are debugging:
(gdb) list
Before you start the execution of the program you are debugging, gdb
displays the first ten lines of the source code, and any subsequent use of this command lists another ten lines. Once you start the execution, gdb
displays the lines that are surrounding the line on which the execution stops, typically when you set a breakpoint.
You can also display the code that is surrounding a particular line:
(gdb) list
file_name:line_number
Similarly, to display the code that is surrounding the beginning of a particular function:
(gdb) list
file_name:function_name
Note that you can change the number of lines the list
command displays:
(gdb)set
listsize
number
Example 8.4. Listing the Source Code of the fibonacci Binary File
The fibonacci.c
file listed in Example 8.1, “Compiling a C Program With Debugging Information” has exactly 17 lines. Assuming that you have compiled it with debugging information and you want the gdb
utility to be capable of listing the entire source code, you can run the following command to change the number of listed lines to 20:
(gdb) set listsize 20
You can now display the entire source code of the file you are debugging by running the list
command with no additional arguments:
(gdb) list
1 #include <stdio.h>
2 #include <limits.h>
3
4 int main (int argc, char *argv[]) {
5 unsigned long int a = 0;
6 unsigned long int b = 1;
7 unsigned long int sum;
8
9 while (b < LONG_MAX) {
10 printf("%ld ", b);
11 sum = a + b;
12 a = b;
13 b = sum;
14 }
15
16 return 0;
17 }
8.5. Setting Breakpoints
Setting a New Breakpoint
To set a new breakpoint at a certain line:
(gdb) break
file_name:line_number
You can also set a breakpoint on a certain function:
(gdb) break
file_name:function_name
Example 8.5. Setting a New Breakpoint
This example assumes that you have compiled the fibonacci.c
file listed in Example 8.1, “Compiling a C Program With Debugging Information” with debugging information.
Set a new breakpoint at line 10:
(gdb) break 10
Breakpoint 1 at 0x4004e5: file fibonacci.c, line 10.
Listing Breakpoints
To display a list of currently set breakpoints:
(gdb)info
breakpoints
Example 8.6. Listing Breakpoints
This example assumes that you have followed the instructions in Example 8.5, “Setting a New Breakpoint”.
Display the list of currently set breakpoints:
(gdb) info breakpoints
Num Type Disp Enb Address What
1 breakpoint keep y 0x00000000004004e5 in main at fibonacci.c:10
Deleting Existing Breakpoints
To delete a breakpoint that is set at a certain line:
(gdb) clear
line_number
Similarly, to delete a breakpoint that is set on a certain function:
(gdb) clear
function_name
Example 8.7. Deleting an Existing Breakpoint
This example assumes that you have compiled the fibonacci.c
file listed in Example 8.1, “Compiling a C Program With Debugging Information” with debugging information.
Set a new breakpoint at line 7:
(gdb) break 7
Breakpoint 2 at 0x4004e3: file fibonacci.c, line 7.
Remove this breakpoint:
(gdb) clear 7
Deleted breakpoint 2
8.6. Starting Execution
To start an execution of the program you are debugging:
(gdb) run
If the program accepts any command line arguments, you can provide them as arguments to the run
command:
(gdb) run
argument…
The execution stops when the first breakpoint (if any) is reached, when an error occurs, or when the program terminates.
Example 8.8. Executing the fibonacci Binary File
This example assumes that you have followed the instructions in Example 8.5, “Setting a New Breakpoint”.
Execute the fibonacci
binary file:
(gdb) run
Starting program: /home/john/fibonacci
Breakpoint 1, main (argc=1, argv=0x7fffffffe4d8) at fibonacci.c:10
10 printf("%ld ", b);
8.7. Displaying Current Values
The gdb
utility allows you to display the value of almost anything that is relevant to the program, from a variable of any complexity to a valid expression or even a library function. However, the most common task is to display the value of a variable.
To display the current value of a certain variable:
(gdb) print
variable_name
Example 8.9. Displaying the Current Values of Variables
This example assumes that you have followed the instructions in Example 8.8, “Executing the fibonacci Binary File” and the execution of the fibonacci
binary stopped after reaching the breakpoint at line 10.
Display the current values of variables a
and b
:
(gdb)print a
$1 = 0 (gdb)print b
$2 = 1
8.8. Continuing Execution
To resume the execution of the program you are debugging after it reached a breakpoint:
(gdb) continue
The execution stops again when another breakpoint is reached. To skip a certain number of breakpoints (typically when you are debugging a loop):
(gdb) continue
number
The gdb
utility also allows you to stop the execution after executing a single line of code:
(gdb) step
Finally, you can execute a certain number of lines:
(gdb) step
number
Example 8.10. Continuing the Execution of the fibonacci Binary File
This example assumes that you have followed the instructions in Example 8.8, “Executing the fibonacci Binary File”, and the execution of the fibonacci
binary stopped after reaching the breakpoint at line 10.
Resume the execution:
(gdb) continue
Continuing.
Breakpoint 1, main (argc=1, argv=0x7fffffffe4d8) at fibonacci.c:10
10 printf("%ld ", b);
The execution stops the next time the breakpoint is reached.
Execute the next three lines of code:
(gdb) step 3
13 b = sum;
This allows you to verify the current value of the sum
variable before it is assigned to b
:
(gdb) print sum
$3 = 2
8.9. Additional Resources
For more information about the GNU Debugger and all its features, see the resources listed below.
Installed Documentation
Installing the devtoolset-12-gdb-doc package provides the following documentation in HTML and PDF formats in the /opt/rh/devtoolset-12/root/usr/share/doc/devtoolset-12-gdb-doc-11.2
directory:
- The Debugging with GDB book, which is a copy of the upstream material with the same name. The version of this document exactly corresponds to the version of GDB available in Red Hat Developer Toolset.
- The GDB’s Obsolete Annotations document, which lists the obsolete GDB level 2 annotations.
Online Documentation
- Red Hat Enterprise Linux 7 Developer Guide — The Developer Guide for Red Hat Enterprise Linux 7 provides more information on the GNU Debugger and debugging.
- GDB Documentation — The upstream GDB documentation includes the GDB User Manual and other reference material.
See Also
- Chapter 1, Red Hat Developer Toolset — An overview of Red Hat Developer Toolset and more information on how to install it on your system.
- Chapter 2, GNU Compiler Collection (GCC) — Further information on how to compile programs written in C, C++, and Fortran.
- Chapter 9, strace — Instructions on using the strace utility to monitor system calls that a program uses and signals it receives.
- Chapter 11, memstomp — Instructions on using the memstomp utility to identify calls to library functions with overlapping memory regions that are not allowed by various standards.
Chapter 9. strace
strace is a diagnostic and debugging tool for the command line that can be used to trace system calls that are made and received by a running process. It records the name of each system call, its arguments, and its return value, as well as signals received by the process and other interactions with the kernel, and prints this record to standard error output or a selected file.
Red Hat Developer Toolset is distributed with strace 5.18.
9.1. Installing strace
In Red Hat Enterprise Linux, the strace
utility is provided by the devtoolset-12-strace package and is automatically installed with devtoolset-12-toolchain as described in Section 1.5, “Installing Red Hat Developer Toolset”.
9.2. Using strace
To run the strace
utility on a program you want to analyze:
$ scl enable devtoolset-12 'strace program argument...'
Replace program with the name of the program you want to analyze, and argument with any command line options and arguments you want to supply to this program. Alternatively, you can run the utility on an already running process by using the -p
command line option followed by the process ID:
$ scl enable devtoolset-12 'strace -p process_id'
Note that you can execute any command using the scl
utility, causing it to be run with the Red Hat Developer Toolset binaries used in preference to the Red Hat Enterprise Linux system equivalent. This allows you to run a shell session with Red Hat Developer Toolset strace
as default:
$ scl enable devtoolset-12 'bash'
To verify the version of strace
you are using at any point:
$ which strace
Red Hat Developer Toolset’s strace
executable path will begin with /opt
. Alternatively, you can use the following command to confirm that the version number matches that for Red Hat Developer Toolset strace
:
$ strace -V
9.2.1. Redirecting Output to a File
By default, strace
prints the name of each system call, its arguments and the return value to standard error output. To redirect this output to a file, use the -o
command line option followed by the file name:
$ scl enable devtoolset-12 'strace -o file_name program argument...'
Replace file_name with the name of the file.
Example 9.1. Redirecting Output to a File
Consider a slightly modified version of the fibonacci
file from Example 8.1, “Compiling a C Program With Debugging Information”. This executable file displays the Fibonacci sequence and optionally allows you to specify how many members of this sequence to list. Run the strace
utility on this file and redirect the trace output to fibonacci.log
:
$ scl enable devtoolset-12 'strace -o fibonacci.log ./fibonacci 20'
1 1 2 3 5 8 13 21 34 55 89 144 233 377 610 987 1597 2584 4181 6765
This creates a new plain-text file called fibonacci.log
in the current working directory.
9.2.2. Tracing Selected System Calls
To trace only a selected set of system calls, run the strace
utility with the -e
command line option:
$ scl enable devtoolset-12 'strace -e expression program argument...'
Replace expression with a comma-separated list of system calls to trace or any of the keywords listed in Table 9.1, “Commonly Used Values of the -e Option”. For a detailed description of all available values, see the strace(1) manual page.
Value | Description |
---|---|
| System calls that accept a file name as an argument. |
| System calls that are related to process management. |
| System calls that are related to networking. |
| System calls that are related to signal management. |
| System calls that are related to inter-process communication (IPC). |
| System calls that are related to file descriptors. |
Note that the syntax -e expression
is a shorthand for the full form -e trace=expression
.
Example 9.2. Tracing Selected System Calls
Consider the employee
file from Example 11.1, “Using memstomp”. Run the strace
utility on this executable file and trace only the mmap
and munmap
system calls:
$ scl enable devtoolset-12 'strace -e mmap,munmap ./employee'
mmap(NULL, 4096, PROT_READ|PROT_WRITE, MAP_PRIVATE|MAP_ANONYMOUS, -1, 0) = 0x7f896c744000
mmap(NULL, 61239, PROT_READ, MAP_PRIVATE, 3, 0) = 0x7f896c735000
mmap(0x3146a00000, 3745960, PROT_READ|PROT_EXEC, MAP_PRIVATE|MAP_DENYWRITE, 3, 0) = 0x3146a00000
mmap(0x3146d89000, 20480, PROT_READ|PROT_WRITE, MAP_PRIVATE|MAP_FIXED|MAP_DENYWRITE, 3, 0x189000) = 0x3146d89000
mmap(0x3146d8e000, 18600, PROT_READ|PROT_WRITE, MAP_PRIVATE|MAP_FIXED|MAP_ANONYMOUS, -1, 0) = 0x3146d8e000
mmap(NULL, 4096, PROT_READ|PROT_WRITE, MAP_PRIVATE|MAP_ANONYMOUS, -1, 0) = 0x7f896c734000
mmap(NULL, 4096, PROT_READ|PROT_WRITE, MAP_PRIVATE|MAP_ANONYMOUS, -1, 0) = 0x7f896c733000
mmap(NULL, 4096, PROT_READ|PROT_WRITE, MAP_PRIVATE|MAP_ANONYMOUS, -1, 0) = 0x7f896c732000
munmap(0x7f896c735000, 61239) = 0
mmap(NULL, 4096, PROT_READ|PROT_WRITE, MAP_PRIVATE|MAP_ANONYMOUS, -1, 0) = 0x7f896c743000
John,john@example.comDoe,
+++ exited with 0 +++
9.2.3. Displaying Time Stamps
To prefix each line of the trace with the exact time of the day in hours, minutes, and seconds, run the strace
utility with the -t
command line option:
$ scl enable devtoolset-12 'strace -t program argument...'
To also display milliseconds, supply the -t
option twice:
$ scl enable devtoolset-12 'strace -tt program argument...'
To prefix each line of the trace with the time required to execute the respective system call, use the -r
command line option:
$ scl enable devtoolset-12 'strace -r program argument...'
Example 9.3. Displaying Time Stamps
Consider an executable file named pwd
. Run the strace
utility on this file and include time stamps in the output:
$ scl enable devtoolset-12 'strace -tt pwd'
19:43:28.011815 execve("./pwd", ["./pwd"], [/* 36 vars */]) = 0
19:43:28.012128 brk(0) = 0xcd3000
19:43:28.012174 mmap(NULL, 4096, PROT_READ|PROT_WRITE, MAP_PRIVATE|MAP_ANONYMOUS, -1, 0) = 0x7fc869cb0000
19:43:28.012427 open("/etc/ld.so.cache", O_RDONLY) = 3
19:43:28.012446 fstat(3, {st_mode=S_IFREG|0644, st_size=61239, ...}) = 0
19:43:28.012464 mmap(NULL, 61239, PROT_READ, MAP_PRIVATE, 3, 0) = 0x7fc869ca1000
19:43:28.012483 close(3) = 0
...
19:43:28.013410 +++ exited with 0 +++
9.2.4. Displaying a Summary
To display a summary of how much time was required to execute each system call, how many times were these system calls executed, and how many errors were encountered during their execution, run the strace
utility with the -c
command line option:
$ scl enable devtoolset-12 'strace -c program argument...'
Example 9.4. Displaying a Summary
Consider an executable file named lsblk
. Run the strace
utility on this file and display a trace summary:
$ scl enable devtoolset-12 'strace -c lsblk > /dev/null'
% time seconds usecs/call calls errors syscall
------ ----------- ----------- --------- --------- ----------------
80.88 0.000055 1 106 16 open
19.12 0.000013 0 140 munmap
0.00 0.000000 0 148 read
0.00 0.000000 0 1 write
0.00 0.000000 0 258 close
0.00 0.000000 0 37 2 stat
...
------ ----------- ----------- --------- --------- ----------------
100.00 0.000068 1790 35 total
9.2.5. Tampering with System Call Results
Simulating errors returned from system calls can help identify missing error handling in programs.
To make a program receive a generic error as the result of a particular system call, run the strace
utility with the -e fault=
option and supply the system call:
$ scl enable devtoolset-12 'strace -e fault=syscall program argument...'
To specify the error type or return value, use the -e inject=
option:
$scl enable devtoolset-12 'strace -e inject=syscall:error=error-type program argument'
$scl enable devtoolset-12 'strace -e inject=syscall:retval=return-value program argument'
Note that specifying the error type and return value is mutually exclusive.
Example 9.5. Tampering with System Call Results
Consider an executable file named lsblk
. Run the strace
utility on this file and make the mmap()
system call return an error:
$ scl enable devtoolset-12 'strace -e fault=mmap:error=EPERM lsblk > /dev/null'
execve("/usr/bin/lsblk", ["lsblk"], 0x7fff1c0e02a0 /* 54 vars */) = 0
brk(NULL) = 0x55d9e8b43000
mmap(NULL, 8192, PROT_READ|PROT_WRITE, MAP_PRIVATE|MAP_ANONYMOUS, -1, 0) = -1 EPERM (Operation not permitted) (INJECTED)
writev(2, [{iov_base="lsblk", iov_len=5}, {iov_base=": ", iov_len=2}, {iov_base="error while loading shared libra"..., iov_len=36}, {iov_base=": ", iov_len=2}, {iov_base="", iov_len=0}, {iov_base="", iov_len=0}, {iov_base="cannot create cache for search p"..., iov_len=35}, {iov_base=": ", iov_len=2}, {iov_base="Cannot allocate memory", iov_len=22}, {iov_base="\n", iov_len=1}], 10lsblk: error while loading shared libraries: cannot create cache for search path: Cannot allocate memory
) = 105
exit_group(127) = ?
+++ exited with 127 +++
9.3. Additional Resources
For more information about strace and its features, see the resources listed below.
Installed Documentation
strace(1) — The manual page for the
strace
utility provides detailed information about its usage. To display the manual page for the version included in Red Hat Developer Toolset:$
scl enable devtoolset-12 'man strace'
See Also
- Chapter 1, Red Hat Developer Toolset — An overview of Red Hat Developer Toolset and more information on how to install it on your system.
- Chapter 10, ltrace — Instructions on tracing program library calls using the ltrace tool.
- Chapter 8, GNU Debugger (GDB) — Instructions on debugging programs written in C, C++, and Fortran.
- Chapter 11, memstomp — Instructions on using the memstomp utility to identify calls to library functions with overlapping memory regions that are not allowed by various standards.
Chapter 10. ltrace
ltrace is a diagnostic and debugging tool for the command line that can be used to display calls that are made to shared libraries. It uses the dynamic library hooking mechanism, which prevents it from tracing calls to statically linked libraries. ltrace also displays return values of the library calls. The output is printed to standard error output or to a selected file.
Red Hat Developer Toolset is distributed with ltrace 0.7.91. While the base version ltrace remains the same as in the previous release of Red Hat Developer Toolset, various enhancements and bug fixes have ported.
10.1. Installing ltrace
In Red Hat Enterprise Linux, the ltrace
utility is provided by the devtoolset-12-ltrace package and is automatically installed with devtoolset-12-toolchain as described in Section 1.5, “Installing Red Hat Developer Toolset”.
10.2. Using ltrace
To run the ltrace
utility on a program you want to analyze:
$ scl enable devtoolset-12 'ltrace program argument...'
Replace program with the name of the program you want to analyze, and argument with any command line options and arguments you want to supply to this program. Alternatively, you can run the utility on an already running process by using the -p
command line option followed by the process ID:
$ scl enable devtoolset-12 'ltrace -p process_id'
Note that you can execute any command using the scl
utility, causing it to be run with the Red Hat Developer Toolset binaries used in preference to the Red Hat Enterprise Linux system equivalent. This allows you to run a shell session with Red Hat Developer Toolset ltrace
as default:
$ scl enable devtoolset-12 'bash'
To verify the version of ltrace
you are using at any point:
$ which ltrace
Red Hat Developer Toolset’s ltrace
executable path will begin with /opt
. Alternatively, you can use the following command to confirm that the version number matches that for Red Hat Developer Toolset ltrace
:
$ ltrace -V
10.2.1. Redirecting Output to a File
By default, ltrace
prints the name of each system call, its arguments and the return value to standard error output. To redirect this output to a file, use the -o
command line option followed by the file name:
$ scl enable devtoolset-12 'ltrace -o file_name program argument...'
Replace file_name with the name of the file.
Example 10.1. Redirecting Output to a File
Consider a slightly modified version of the fibonacci
file from Example 8.1, “Compiling a C Program With Debugging Information”. This executable file displays the Fibonacci sequence and optionally allows you to specify how many members of this sequence to list. Run the ltrace
utility on this file and redirect the trace output to fibonacci.log
:
$ scl enable devtoolset-12 'ltrace -o fibonacci.log ./fibonacci 20'
1 1 2 3 5 8 13 21 34 55 89 144 233 377 610 987 1597 2584 4181 6765
This creates a new plain-text file called fibonacci.log
in the current working directory.
10.2.2. Tracing Selected Library Calls
To trace only a selected set of library calls, run the ltrace
utility with the -e
command line option:
$ scl enable devtoolset-12 'ltrace -e expression program argument...'
Replace expression with a chain of rules to specify the library calls to trace. The rules can consist of patterns that identify symbol names (such as malloc
or free
) and patterns that identify library SONAMEs (such as libc.so
). For example, to trace call to the malloc
and free
function but to omit those that are done by the libc
library:
$ scl enable devtoolset-12 'ltrace -e malloc+free-@libc.so* program'
Example 10.2. Tracing Selected Library Calls
Consider the ls
command. Run the ltrace
utility on this program and trace only the opendir
, readdir
, and closedir
function calls:
$ scl enable devtoolset-12 'ltrace -e opendir+readdir+closedir ls'
ls->opendir(".") = { 3 }
ls->readdir({ 3 }) = { 61533, "." }
ls->readdir({ 3 }) = { 131, ".." }
ls->readdir({ 3 }) = { 67185100, "BUILDROOT" }
ls->readdir({ 3 }) = { 202390772, "SOURCES" }
ls->readdir({ 3 }) = { 60249, "SPECS" }
ls->readdir({ 3 }) = { 67130110, "BUILD" }
ls->readdir({ 3 }) = { 136599168, "RPMS" }
ls->readdir({ 3 }) = { 202383274, "SRPMS" }
ls->readdir({ 3 }) = nil
ls->closedir({ 3 }) = 0
BUILD BUILDROOT RPMS SOURCES SPECS SRPMS
+++ exited (status 0) +++
For a detailed description of available filter expressions, see the ltrace(1) manual page.
10.2.3. Displaying Time Stamps
To prefix each line of the trace with the exact time of the day in hours, minutes, and seconds, run the ltrace
utility with the -t
command line option:
$ scl enable devtoolset-12 'ltrace -t program argument...'
To also display milliseconds, supply the -t
option twice:
$ scl enable devtoolset-12 'ltrace -tt program argument...'
To prefix each line of the trace with the time required to execute the respective system call, use the -r
command line option:
$ scl enable devtoolset-12 'ltrace -r program argument...'
Example 10.3. Displaying Time Stamps
Consider the pwd
command. Run the ltrace
utility on this program and include time stamps in the output:
$ scl enable devtoolset-12 'ltrace -tt pwd'
13:27:19.631371 __libc_start_main([ "pwd" ] <unfinished ...>
13:27:19.632240 getenv("POSIXLY_CORRECT") = nil
13:27:19.632520 strrchr("pwd", '/') = nil
13:27:19.632786 setlocale(LC_ALL, "") = "en_US.UTF-8"
13:27:19.633220 bindtextdomain("coreutils", "/usr/share/locale") = "/usr/share/locale"
13:27:19.633471 textdomain("coreutils") = "coreutils"
(...)
13:27:19.637110 exited (status 0)
10.2.4. Displaying a Summary
To display a summary of how much time was required to execute each system call and how many times were these system calls executed, run the ltrace
utility with the -c
command line option:
$ scl enable devtoolset-12 'ltrace -c program argument...'
Example 10.4. Displaying a Summary
Consider the lsblk
command. Run the ltrace
utility on this program and display a trace summary:
$ scl enable devtoolset-12 'ltrace -c lsblk > /dev/null'
% time seconds usecs/call calls function
------ ----------- ----------- --------- --------------------
53.60 0.261644 261644 1 __libc_start_main
4.48 0.021848 58 374 mbrtowc
4.41 0.021524 57 374 wcwidth
4.39 0.021409 57 374 __ctype_get_mb_cur_max
4.38 0.021359 57 374 iswprint
4.06 0.019838 74 266 readdir64
3.21 0.015652 69 224 strlen
...
------ ----------- ----------- --------- --------------------
100.00 0.488135 3482 total
10.3. Additional Resources
For more information about ltrace and its features, see the resources listed below.
Installed Documentation
ltrace(1) — The manual page for the
ltrace
utility provides detailed information about its usage. To display the manual page for the version included in Red Hat Developer Toolset:$
scl enable devtoolset-12 'man ltrace'
Online Documentation
- ltrace for RHEL 6 and 7 — This article on the Red Hat Developer Blog offers additional in-depth information (including practical examples) on how to use ltrace for application debugging.
See Also
- Chapter 1, Red Hat Developer Toolset — An overview of Red Hat Developer Toolset and more information on how to install it on your system.
- Chapter 9, strace — Instructions on tracing program system calls using the strace tool.
- Chapter 8, GNU Debugger (GDB) — Instructions on debugging programs written in C, C++, and Fortran.
- Chapter 11, memstomp — Instructions on using the memstomp utility to identify calls to library functions with overlapping memory regions that are not allowed by various standards.
Chapter 11. memstomp
memstomp is a command line tool that can be used to identify function calls with overlapping memory regions in situations when such an overlap is not permitted by various standards. It intercepts calls to the library functions listed in Table 11.1, “Function Calls Inspected by memstomp” and for each memory overlap, it displays a detailed backtrace to help you debug the problem.
Similarly to Valgrind, the memstomp
utility inspects applications without the need to recompile them. However, it is much faster than this tool and therefore serves as a convenient alternative to it.
Red Hat Developer Toolset is distributed with memstomp 0.1.5.
Function | Description |
---|---|
| Copies n bytes from one memory area to another and returns a pointer to the second memory area. |
| Copies a maximum of n bytes from one memory area to another and stops when a certain character is found. It either returns a pointer to the byte following the last written byte, or NULL if the given character is not found. |
| Copies n bytes from one memory area to another and returns a pointer to the byte following the last written byte. |
| Copies a string from one memory area to another and returns a pointer to the second string. |
| Copies a string from one memory area to another and returns a pointer to the terminating null byte of the second string. |
| Copies a maximum of n characters from one string to another and returns a pointer to the second string. |
| Copies a maximum of n characters from one string to another. It either returns a pointer to the terminating null byte of the second string, or if the string is not null-terminated, a pointer to the byte following the last written byte. |
| Appends one string to another while overwriting the terminating null byte of the second string and adding a new one at its end. It returns a pointer to the new string. |
| Appends a maximum of n characters from one string to another while overwriting the terminating null byte of the second string and adding a new one at its end. It returns a pointer to the new string. |
|
The wide-character equivalent of the |
|
The wide-character equivalent of the |
|
The wide-character equivalent of the |
|
The wide-character equivalent of the |
|
The wide-character equivalent of the |
|
The wide-character equivalent of the |
11.1. Installing memstomp
In Red Hat Developer Toolset, the memstomp
utility is provided by the devtoolset-12-memstomp package and is automatically installed with devtoolset-12-toolchain as described in Section 1.5, “Installing Red Hat Developer Toolset”.
11.2. Using memstomp
To run the memstomp
utility on a program you want to analyze:
$ scl enable devtoolset-12 'memstomp program argument...'
To immediately terminate the analyzed program when a problem is detected, run the utility with the --kill
(or -k
for short) command line option:
$ scl enable devtoolset-12 'memstomp --kill program argument...'
The use of the --kill
option is especially recommended if you are analyzing a multi-threaded program; the internal implementation of backtraces is not thread-safe and running the memstomp
utility on a multi-threaded program without this command line option can therefore produce unreliable results.
Additionally, if you have compiled the analyzed program with the debugging information or this debugging information is available to you, you can use the --debug-info
(or -d
) command line option to produce a more detailed backtrace:
$ scl enable devtoolset-12 'memstomp --debug-info program argument...'
For detailed instructions on how to compile your program with the debugging information built in the binary file, see Section 8.2, “Preparing a Program for Debugging”. For information on how to install debugging information for any of the Red Hat Developer Toolset packages, see Section 1.5.4, “Installing Debugging Information”.
Note that you can execute any command using the scl
utility, causing it to be run with the Red Hat Developer Toolset binaries used in preference to the Red Hat Enterprise Linux system equivalent. This allows you to run a shell session with Red Hat Developer Toolset memstomp
as default:
$ scl enable devtoolset-12 'bash'
Example 11.1. Using memstomp
In the current working directory, create a source file named employee.c
with the following contents:
#include <stdio.h> #include <string.h> #define BUFSIZE 80 int main(int argc, char *argv[]) { char employee[BUFSIZE] = "John,Doe,john@example.com"; char name[BUFSIZE] = {0}; char surname[BUFSIZE] = {0}; char *email; size_t length; /* Extract the information: */ memccpy(name, employee, ',', BUFSIZE); length = strlen(name); memccpy(surname, employee + length, ',', BUFSIZE); length += strlen(surname); email = employee + length; /* Compose the new entry: */ strcat(employee, surname); strcpy(employee, name); strcat(employee, email); /* Print the result: */ puts(employee); return 0; }
Compile this program into a binary file named employee
:
$ scl enable devtoolset-12 'gcc -rdynamic -g -o employee employee.c'
To identify erroneous function calls with overlapping memory regions:
$ scl enable devtoolset-12 'memstomp --debug-info ./employee'
memstomp: 0.1.4 successfully initialized for process employee (pid 14887).
strcat(dest=0x7fff13afc265, src=0x7fff13afc269, bytes=21) overlap for employee(14887)
??:0 strcpy()
??:0 strcpy()
??:0 _Exit()
??:0 strcat()
employee.c:26 main()
??:0 __libc_start_main()
??:0 _start()
John,john@example.comDoe,
11.3. Additional Resources
For more information about memstomp
and its features, see the resources listed below.
Installed Documentation
memstomp(1) — The manual page for the
memstomp
utility provides detailed information about its usage. To display the manual page for the version included in Red Hat Developer Toolset:$
scl enable devtoolset-12 'man memstomp'
See Also
- Chapter 1, Red Hat Developer Toolset — An overview of Red Hat Developer Toolset and more information on how to install it on your system.
- Chapter 8, GNU Debugger (GDB) — Instructions on debugging programs written in C, C++, and Fortran.
- Chapter 9, strace — Instructions on using the strace utility to monitor system calls that a program uses and signals it receives.
- Chapter 13, Valgrind — Instructions on using the Valgrind tool to profile applications and detect memory errors and memory management problems, such as the use of uninitialized memory, improper allocation and freeing of memory, and the use of improper arguments in system calls.
Part IV. Performance Monitoring Tools
Chapter 12. SystemTap
SystemTap is a tracing and probing tool that allows users to monitor the activities of the entire system without needing to instrument, recompile, install, and reboot. It is programmable with a custom scripting language, which gives it expressiveness (to trace, filter, and analyze) and reach (to look into the running kernel and applications).
SystemTap can monitor various types of events, such as function calls within the kernel or applications, timers, tracepoints, performance counters, and so on. Some included example scripts produce output similar to netstat
, ps
, top
, and iostat
, others include pretty-printed function callgraph traces or tools for working around security bugs.
Red Hat Developer Toolset is distributed with SystemTap 4.7. This version is more recent than the version included in the previous release of Red Hat Developer Toolset and provides numerous bug fixes and enhancements.
Name | Description |
---|---|
| Translates probing instructions into C code, builds a kernel module, and loads it into a running Linux kernel. |
| The Dyninst backend for SystemTap. |
|
Loads, unloads, attaches to, and detaches from kernel modules built with the |
| Serves as a remote shell for SystemTap. |
| Determines and—if possible—downloads the kernel information packages that are required to run SystemTap. |
|
Merges per-CPU files. This script is automatically executed when the |
| Gathers important information about the system for the purpose of reporting a bug in SystemTap. |
|
A compile server, which listens for requests from |
12.1. Installing SystemTap
In Red Hat Developer Toolset, SystemTap
is provided by the devtoolset-12-systemtap package and is automatically installed with devtoolset-12-perftools as described in Section 1.5, “Installing Red Hat Developer Toolset”.
In order to place instrumentation into the Linux kernel, SystemTap may also require installation of additional packages with debugging information. To determine which packages to install, run the stap-prep
utility as follows:
$ scl enable devtoolset-12 'stap-prep'
Note that if you execute this command as the root
user, the utility automatically offers the packages for installation. For more information on how to install these packages on your system, see the Red Hat Enterprise Linux 7 SystemTap Beginners Guide.
12.2. Using SystemTap
To execute any of the tools that are part of SystemTap:
$ scl enable devtoolset-12 'tool option...'
See Table 12.1, “Tools Distributed with SystemTap for Red Hat Developer Toolset” for a list of tools that are distributed with SystemTap. For example, to run the stap
tool to build an instrumentation module:
$ scl enable devtoolset-12 'stap option... argument...'
Note that you can execute any command using the scl
utility, causing it to be run with the Red Hat Developer Toolset binaries used in preference to the Red Hat Enterprise Linux system equivalent. This allows you to run a shell session with Red Hat Developer Toolset SystemTap as default:
$ scl enable devtoolset-12 'bash'
To verify the version of SystemTap you are using at any point:
$ which stap
Red Hat Developer Toolset’s stap
executable path will begin with /opt
. Alternatively, you can use the following command to confirm that the version number matches that for Red Hat Developer Toolset SystemTap:
$ stap -V
12.3. Additional Resources
For more information about SystemTap and its features, see the resources listed below.
Installed Documentation
stap(1) — The manual page for the
stap
command provides detailed information on its usage, as well as references to other related manual pages. To display the manual page for the version included in Red Hat Developer Toolset:$
scl enable devtoolset-12 'man stap'
staprun(8) — The manual page for the
staprun
command provides detailed information on its usage. To display the manual page for the version included in Red Hat Developer Toolset:$
scl enable devtoolset-12 'man staprun'
Online Documentation
- Red Hat Enterprise Linux 7 SystemTap Beginners Guide — The SystemTap Beginners Guide for Red Hat Enterprise Linux 7 provides an introduction to SystemTap and its usage.
- Red Hat Enterprise Linux 7 SystemTap Tapset Reference — The SystemTap Tapset Reference for Red Hat Enterprise Linux 7 provides further details about SystemTap.
- The SystemTap Documentation — The SystemTap documentation provides further documentation about SystemTap, and numerous examples of the SystemTap scripts.
See Also
- Chapter 1, Red Hat Developer Toolset — An overview of Red Hat Developer Toolset and more information on how to install it on your system.
- Chapter 13, Valgrind — Instructions on using the Valgrind tool to profile applications and detect memory errors and memory management problems, such as the use of uninitialized memory, improper allocation and freeing of memory, and the use of improper arguments in system calls.
- Chapter 14, OProfile — Instructions on using the OProfile tool to determine which sections of code consume the greatest amount of CPU time and why.
- Chapter 15, Dyninst — Instructions on using the Dyninst library to instrument a user-space executable.
Chapter 13. Valgrind
Valgrind is an instrumentation framework that ships with a number of tools for profiling applications. It can be used to detect various memory errors and memory-management problems, such as the use of uninitialized memory or an improper allocation and freeing of memory, or to identify the use of improper arguments in system calls. For a complete list of profiling tools that are distributed with the Red Hat Developer Toolset version of Valgrind, see Table 13.1, “Tools Distributed with Valgrind for Red Hat Developer Toolset”.
Valgrind profiles an application by rewriting it and instrumenting the rewritten binary. This allows you to profile your application without the need to recompile it, but it also makes Valgrind significantly slower than other profilers, especially when performing extremely detailed runs. It is therefore not suited to debugging time-specific issues, or kernel-space debugging.
Red Hat Developer Toolset is distributed with Valgrind 3.19.0. This version is more recent than the version included in the previous release of Red Hat Developer Toolset and provides numerous bug fixes and enhancements.
Name | Description |
---|---|
Memcheck | Detects memory management problems by intercepting system calls and checking all read and write operations. |
Cachegrind | Identifies the sources of cache misses by simulating the level 1 instruction cache (I1), level 1 data cache (D1), and unified level 2 cache (L2). |
Callgrind | Generates a call graph representing the function call history. |
Helgrind | Detects synchronization errors in multithreaded C, C++, and Fortran programs that use POSIX threading primitives. |
DRD | Detects errors in multithreaded C and C++ programs that use POSIX threading primitives or any other threading concepts that are built on top of these POSIX threading primitives. |
Massif | Monitors heap and stack usage. |
13.1. Installing Valgrind
In Red Hat Developer Toolset, Valgrind is provided by the devtoolset-12-valgrind package and is automatically installed with devtoolset-12-perftools.
For detailed instructions on how to install Red Hat Developer Toolset and related packages to your system, see Section 1.5, “Installing Red Hat Developer Toolset”.
Note that if you use Valgrind in combination with the GNU Debugger, it is recommended that you use the version of GDB that is included in Red Hat Developer Toolset to ensure that all features are fully supported.
13.2. Using Valgrind
To run any of the Valgrind tools on a program you want to profile:
$ scl enable devtoolset-12 'valgrind --tool=tool program argument...'
See Table 13.1, “Tools Distributed with Valgrind for Red Hat Developer Toolset” for a list of tools that are distributed with Valgrind. The argument of the --tool
command line option must be specified in lower case, and if this option is omitted, Valgrind uses Memcheck by default. For example, to run Cachegrind on a program to identify the sources of cache misses:
$ scl enable devtoolset-12 'valgrind --tool=cachegrind program argument...'
Note that you can execute any command using the scl
utility, causing it to be run with the Red Hat Developer Toolset binaries used in preference to the Red Hat Enterprise Linux system equivalent. This allows you to run a shell session with Red Hat Developer Toolset Valgrind as default:
$ scl enable devtoolset-12 'bash'
To verify the version of Valgrind you are using at any point:
$ which valgrind
Red Hat Developer Toolset’s valgrind
executable path will begin with /opt
. Alternatively, you can use the following command to confirm that the version number matches that for Red Hat Developer Toolset Valgrind:
$ valgrind --version
13.3. Additional Resources
For more information about Valgrind and its features, see the resources listed below.
Installed Documentation
valgrind(1) — The manual page for the
valgrind
utility provides detailed information on how to use Valgrind. To display the manual page for the version included in Red Hat Developer Toolset:$
scl enable devtoolset-12 'man valgrind'
-
Valgrind Documentation — HTML documentation for Valgrind is located at
/opt/rh/devtoolset-12/root/usr/share/doc/devtoolset-12-valgrind-3.19.0/html/index.html
.
Online Documentation
- Red Hat Enterprise Linux 7 Developer Guide — The Developer Guide for Red Hat Enterprise Linux 7 provides more information about Valgrind and its Eclipse plug-in.
- Red Hat Enterprise Linux 7 Performance Tuning Guide — The Performance Tuning Guide for Red Hat Enterprise Linux 7 provide more detailed information about using Valgrind to profile applications.
See Also
- Chapter 1, Red Hat Developer Toolset — An overview of Red Hat Developer Toolset and more information on how to install it on your system.
- Chapter 11, memstomp — Instructions on using the memstomp utility to identify calls to library functions with overlapping memory regions that are not allowed by various standards.
- Chapter 12, SystemTap — An introduction to the SystemTap tool and instructions on how to use it to monitor the activities of a running system.
- Chapter 14, OProfile — Instructions on using the OProfile tool to determine which sections of code consume the greatest amount of CPU time and why.
- Chapter 15, Dyninst — Instructions on using the Dyninst library to instrument a user-space executable.
Chapter 14. OProfile
OProfile is a low overhead, system-wide profiler that uses the performance-monitoring hardware on the processor to retrieve information about the kernel and executables on the system, such as when memory is referenced, the number of level 2 cache (L2) requests, and the number of hardware interrupts received. It consists of a configuration utility, a daemon for collecting data, and a number of tools that can be used to transform the data into a human-readable form. For a complete list of tools that are distributed with the Red Hat Developer Toolset version of OProfile, see Table 14.1, “Tools Distributed with OProfile for Red Hat Developer Toolset”.
OProfile profiles an application without adding any instrumentation by recording the details of every nth event. This allows it to consume fewer resources than Valgrind, but it also causes its samples to be less precise. Unlike Valgrind, which only collects data for a single process and its children in user-space, OProfile is well suited to collect system-wide data on both user-space and kernel-space processes, and requires root
privileges to run.
Red Hat Developer Toolset is distributed with OProfile 1.4.0.
Name | Description |
---|---|
| Records samples either for a single process or system-wide using the Linux Performance Events subsystem. |
| Generates an annotated source file or assembly listing from the profiling data. |
| Generates a directory containing executable, debug, and sample files. |
|
Generates a summary of a profiling session in a format compatible with |
| Displays a list of available events. |
| Converts a sample database file from a foreign binary format to the native format. |
| Converts a just-in-time (JIT) dump file to the Executable and Linkable Format (ELF). |
| Generates image and symbol summaries of a profiling session. |
| A new tool for counting the number of times particular events occur during the duration of a monitored command. |
14.1. Installing OProfile
In Red Hat Developer Toolset, OProfile is provided by the devtoolset-12-oprofile package and is automatically installed with devtoolset-12-perftools as described in Section 1.5, “Installing Red Hat Developer Toolset”.
14.2. Using OProfile
To run any of the tools that are distributed with OProfile:
# scl enable devtoolset-12 'tool option...'
See Table 14.1, “Tools Distributed with OProfile for Red Hat Developer Toolset” for a list of tools that are distributed with OProfile. For example, to use the ophelp
command to list available events in the XML format:
$ scl enable devtoolset-12 'ophelp -X'
Note that you can execute any command using the scl
utility, causing it to be run with the Red Hat Developer Toolset binaries used in preference to the Red Hat Enterprise Linux system equivalent. This allows you to run a shell session with Red Hat Developer Toolset OProfile as default:
$ scl enable devtoolset-12 'bash'
To verify the version of OProfile you are using at any point:
$ which operf
Red Hat Developer Toolset’s operf
executable path will begin with /opt
. Alternatively, you can use the following command to confirm that the version number matches that for Red Hat Developer Toolset OProfile:
# operf --version
14.3. Additional Resources
For more information about OProfile and its features, see the resources listed below.
Installed Documentation
oprofile(1) — The manual page named oprofile provides an overview of OProfile and available tools. To display the manual page for the version included in Red Hat Developer Toolset:
$
scl enable devtoolset-12 'man oprofile'
opannotate(1), oparchive(1), operf(1), opgprof(1), ophelp(1), opimport(1), opreport(1) — Manual pages for various tools distributed with OProfile provide more information on their respective usage. To display the manual page for the version included in Red Hat Developer Toolset:
scl enable devtoolset-12 'man tool'
Online Documentation
- Red Hat Enterprise Linux 7 Developer Guide — The Developer Guide for Red Hat Enterprise Linux 7 provides more information on OProfile.
-
Red Hat Enterprise Linux 7 System Administrator’s Guide — The System Administrator’s Guide for Red Hat Enterprise Linux 7 documents how to use the
operf
tool.
See Also
- Chapter 1, Red Hat Developer Toolset — An overview of Red Hat Developer Toolset and more information on how to install it on your system.
- Chapter 12, SystemTap — An introduction to SystemTap and instructions on how to use it to monitor the activities of a running system.
- Chapter 13, Valgrind — Instructions on using the Valgrind tool to profile applications and detect memory errors and memory management problems, such as the use of uninitialized memory, improper allocation and freeing of memory, and the use of improper arguments in system calls.
- Chapter 15, Dyninst — Instructions on using the Dyninst library to instrument a user-space executable.
Chapter 15. Dyninst
The Dyninst library provides an application programming interface (API) for instrumenting and working with user-space executables during their execution. It can be used to insert code into a running program, change certain subroutine calls, or even remove them from the program. It serves as a valuable debugging and performance-monitoring tool. The Dyninst API is also commonly used along with SystemTap to allow non-root
users to instrument user-space executables.
Red Hat Developer Toolset is distributed with Dyninst 12.1.0.
15.1. Installing Dyninst
In Red Hat Developer Toolset, the Dyninst library is provided by the devtoolset-12-dyninst package and is automatically installed with devtoolset-12-perftools as described in Section 1.5, “Installing Red Hat Developer Toolset”. In addition, it is recommended that you also install the GNU Compiler Collection provided by the devtoolset-12-toolchain package.
If you intend to write a custom instrumentation for binaries, install the relevant header files:
# yum install devtoolset-12-dyninst-devel
You can also install API documentation for this library:
# yum install devtoolset-12-dyninst-doc
For a complete list of documents that are included in the devtoolset-12-dyninst-doc package, see Section 15.3, “Additional Resources”. For detailed instructions on how to install optional packages to your system, see Section 1.5, “Installing Red Hat Developer Toolset”.
15.2. Using Dyninst
15.2.1. Using Dyninst with SystemTap
To use Dyninst along with SystemTap to allow non-root
users to instrument user-space executables, run the stap
command with the --dyninst
(or --runtime=dyninst
) command line option. This tells stap
to translate a SystemTap script into C code that uses the Dyninst library, compile this C code into a shared library, and then load the shared library and run the script. Note that when executed like this, the stap
command also requires the -c
or -x
command line option to be specified.
To use the Dyninst runtime to instrument an executable file:
$ scl enable devtoolset-12 "stap --dyninst -c 'command' option... argument..."
Similarly, to use the Dyninst runtime to instrument a user’s process:
$ scl enable devtoolset-12 "stap --dyninst -x process_id option... argument..."
See Chapter 12, SystemTap for more information about the Red Hat Developer Toolset version of SystemTap. For a general introduction to SystemTap and its usage, see the SystemTap Beginners Guide for Red Hat Enterprise Linux 7.
Example 15.1. Using Dyninst with SystemTap
Consider a source file named exercise.C
that has the following contents:
#include <stdio.h> void print_iteration(int value) { printf("Iteration number %d\n", value); } int main(int argc, char **argv) { int i; printf("Enter the starting number: "); scanf("%d", &i); for(; i>0; --i) print_iteration(i); return 0; }
This program prompts the user to enter a starting number and then counts down to 1, calling the print_iteration()
function for each iteration in order to print the number to the standard output. Compile this program on the command line using the g++
compiler from Red Hat Developer Toolset:
$ scl enable devtoolset-12 'g++ -g -o exercise exercise.C'
Now consider another source file named count.stp
with the following contents:
#!/usr/bin/stap global count = 0 probe process.function("print_iteration") { count++ } probe end { printf("Function executed %d times.\n", count) }
This SystemTap script prints the total number of times the print_iteration()
function was called during the execution of a process. Run this script on the exercise
binary file:
$scl enable devtoolset-12 "stap --dyninst -c './exercise' count.stp"
Enter the starting number:5
Iteration number 5 Iteration number 4 Iteration number 3 Iteration number 2 Iteration number 1 Function executed 5 times.
15.2.2. Using Dyninst as a Stand-alone Library
Before using the Dyninst library as a part of your application, set the value of the DYNINSTAPI_RT_LIB
environment variable to the path to the runtime library file:
$ export DYNINSTAPI_RT_LIB=/opt/rh/devtoolset-12/root/usr/lib64/dyninst/libdyninstAPI_RT.so
This sets the DYNINSTAPI_RT_LIB
environment variable in the current shell session.
Example 15.2, “Using Dyninst as a Stand-alone Application” illustrates how to write and build a program to monitor the execution of a user-space process. For a detailed explanation of how to use Dyninst, see the resources listed in Section 15.3, “Additional Resources”.
Example 15.2. Using Dyninst as a Stand-alone Application
Consider the exercise.C
source file from Example 15.1, “Using Dyninst with SystemTap”: this program prompts the user to enter a starting number and then counts down to 1, calling the print_iteration()
function for each iteration in order to print the number to standard output.
Now consider another source file named count.C
with the following contents:
#include <stdio.h> #include <fcntl.h> #include "BPatch.h" #include "BPatch_process.h" #include "BPatch_function.h" #include "BPatch_Vector.h" #include "BPatch_thread.h" #include "BPatch_point.h" void usage() { fprintf(stderr, "Usage: count <process_id> <function>\n"); } // Global information for counter BPatch_variableExpr *counter = NULL; void createCounter(BPatch_process *app, BPatch_image *appImage) { int zero = 0; counter = app->malloc(*appImage->findType("int")); counter->writeValue(&zero); } bool interceptfunc(BPatch_process *app, BPatch_image *appImage, char *funcName) { BPatch_Vector<BPatch_function *> func; appImage->findFunction(funcName, func); if(func.size() == 0) { fprintf(stderr, "Unable to find function to instrument()\n"); exit (-1); } BPatch_Vector<BPatch_snippet *> incCount; BPatch_Vector<BPatch_point *> *points; points = func[0]->findPoint(BPatch_entry); if ((*points).size() == 0) { exit (-1); } BPatch_arithExpr counterPlusOne(BPatch_plus, *counter, BPatch_constExpr(1)); BPatch_arithExpr addCounter(BPatch_assign, *counter, counterPlusOne); return app->insertSnippet(addCounter, *points); } void printCount(BPatch_thread *thread, BPatch_exitType) { int val = 0; counter->readValue(&val, sizeof(int)); fprintf(stderr, "Function executed %d times.\n", val); } int main(int argc, char *argv[]) { int pid; BPatch bpatch; if (argc != 3) { usage(); exit(1); } pid = atoi(argv[1]); BPatch_process *app = bpatch.processAttach(NULL, pid); if (!app) exit (-1); BPatch_image *appImage = app->getImage(); createCounter(app, appImage); fprintf(stderr, "Finding function %s(): ", argv[2]); BPatch_Vector<BPatch_function*> countFuncs; fprintf(stderr, "OK\nInstrumenting function %s(): ", argv[2]); interceptfunc(app, appImage, argv[2]); bpatch.registerExitCallback(printCount); fprintf(stderr, "OK\nWaiting for process %d to exit...\n", pid); app->continueExecution(); while (!app->isTerminated()) bpatch.waitForStatusChange(); return 0; }
Note that a client application is expected to destroy all Bpatch
objects before any of the Dyninst library destructors are called. Otherwise the mutator might terminate unexpectedly with a segmentation fault. To work around this problem, set the BPatch
object of the mutator as a local variable in the main()
function. Or, if you need to use BPatch
as a global variable, manually detach all the mutatee processes before the mutator exits.
This program accepts a process ID and a function name as command line arguments and then prints the total number of times the function was called during the execution of the process. You can use the following Makefile
to build these two files:
DTS = /opt/rh/devtoolset-12/root CXXFLAGS = -g -I$(DTS)/usr/include/dyninst LBITS := $(shell getconf LONG_BIT) ifeq ($(LBITS),64) DYNINSTLIBS = $(DTS)/usr/lib64/dyninst else DYNINSTLIBS = $(DTS)/usr/lib/dyninst endif .PHONY: all all: count exercise count: count.C g++ $(CXXFLAGS) count.C -I /usr/include/dyninst -c g++ $(CXXFLAGS) count.o -L $(DYNINSTLIBS) -ldyninstAPI -o count exercise: exercise.C g++ $(CXXFLAGS) exercise.C -o exercise .PHONY: clean clean: rm -rf *~ *.o count exercise
To compile the two programs on the command line using the g++
compiler from Red Hat Developer Toolset, run the make
utility:
$ scl enable devtoolset-12 make
g++ -g -I/opt/rh/devtoolset-12/root/usr/include/dyninst count.C -c
g++ -g -I/opt/rh/devtoolset-12/root/usr/include/dyninst count.o -L /opt/rh/devtoolset-12/root/usr/lib64/dyninst -ldyninstAPI -o count
g++ -g -I/opt/rh/devtoolset-12/root/usr/include/dyninst exercise.C -o exercise
This creates new binary files called exercise
and count
in the current working directory.
In one shell session, execute the exercise
binary file as follows and wait for it to prompt you to enter the starting number:
$ ./exercise
Enter the starting number:
Do not enter this number. Instead, start another shell session and type the following at its prompt to set the DYNINSTAPI_RT_LIB
environment variable and execute the count
binary file:
$export DYNINSTAPI_RT_LIB=/opt/rh/devtoolset-12/root/usr/lib64/dyninst/libdyninstAPI_RT.so
$./count `pidof exercise` print_iteration
Finding function print_iteration(): OK Instrumenting function print_iteration(): OK Waiting for process 8607 to exit...
Now switch back to the first shell session and enter the starting number as requested by the exercise
program. For example:
Enter the starting number: 5
Iteration number 5
Iteration number 4
Iteration number 3
Iteration number 2
Iteration number 1
When the exercise
program terminates, the count
program displays the number of times the print_iteration()
function was executed:
Function executed 5 times.
15.3. Additional Resources
For more information about Dyninst and its features, see the resources listed below.
Installed Documentation
The devtoolset-12-dyninst-doc package installs the following documents in the /opt/rh/devtoolset-12/root/usr/share/doc/devtoolset-12-dyninst-doc-12.1.0/
directory:
-
Dyninst Programmer’s Guide — A detailed description of the Dyninst API is stored in the
DyninstAPI.pdf
file. -
DynC API Programmer’s Guide — An introduction to DynC API is stored in the
dynC_API.pdf
file. -
ParseAPI Programmer’s Guide — An introduction to the ParseAPI is stored in the
ParseAPI.pdf
file. -
PatchAPI Programmer’s Guide — An introduction to PatchAPI is stored in the
PatchAPI.pdf
file. -
ProcControlAPI Programmer’s Guide — A detailed description of ProcControlAPI is stored in the
ProcControlAPI.pdf
file. -
StackwalkerAPI Programmer’s Guide — A detailed description of StackwalkerAPI is stored in the
stackwalker.pdf
file. -
SymtabAPI Programmer’s Guide — An introduction to SymtabAPI is stored in the
SymtabAPI.pdf
file. -
InstructionAPI Reference Manual — A detailed description of the InstructionAPI is stored in the
InstructionAPI.pdf
file.
For information on how to install this package on your system, see Section 15.1, “Installing Dyninst”.
Online Documentation
- Dyninst Home Page — The project home page provides links to additional documentation and related publications.
- Red Hat Enterprise Linux 7 SystemTap Beginners Guide — The SystemTap Beginners Guide for Red Hat Enterprise Linux 7 provides an introduction to SystemTap and its usage.
- Red Hat Enterprise Linux 7 SystemTap Tapset Reference — The SystemTap Tapset Reference for Red Hat Enterprise Linux 7 provides further details about SystemTap.
See Also
- Chapter 1, Red Hat Developer Toolset — An overview of Red Hat Developer Toolset and more information on how to install it on your system.
- Chapter 12, SystemTap — An introduction to SystemTap and instructions on how to use it to monitor the activities of a running system.
- Chapter 13, Valgrind — Instructions on using the Valgrind tool to profile applications and detect memory errors and memory management problems, such as the use of uninitialized memory, improper allocation and freeing of memory, and the use of improper arguments in system calls.
- Chapter 14, OProfile — Instructions on using the OProfile tool to determine which sections of code consume the greatest amount of CPU time and why.
Part V. Compiler Toolsets
Chapter 16. Compiler Toolsets documentation
The descriptions of the three compiler toolsets:
- LLVM Toolset
- Go Toolset
- Rust Toolset
have been moved to a separate documentation set under Red Hat Developer Tools.
Part VI. Getting Help
Chapter 17. Accessing Red Hat Product Documentation
Red Hat Product Documentation located at https://access.redhat.com/site/documentation/ serves as a central source of information. It is currently translated in 23 languages, and for each product, it provides different kinds of books from release and technical notes to installation, user, and reference guides in HTML, PDF, and EPUB formats.
Below is a brief list of documents that are directly or indirectly relevant to this book.
Red Hat Developer Toolset
- Red Hat Developer Toolset 12.1 Release Notes — The Release Notes for Red Hat Developer Toolset 12.1 contain more information.
- Using Red Hat Software Collections Container Images — The Using Red Hat Software Collections Container Images provides instructions for obtaining, configuring, and using container images that are shipped with Red Hat Software Collections, including the Red Hat Developer Toolset container images.
- Red Hat Software Collections Packaging Guide — The Software Collections Packaging Guide explains the concept of Software Collections and documents how to create, build, and extend them.
Red Hat Enterprise Linux
- Red Hat Enterprise Linux 7 Developer Guide — The Developer Guide for Red Hat Enterprise Linux 7 provides more information about libraries and runtime support, compiling and building, debugging, and profiling.
- Red Hat Enterprise Linux 7 Installation Guide — The Installation Guide for Red Hat Enterprise Linux 7 explains how to obtain, install, and update the system.
- Red Hat Enterprise Linux 7 System Administrator’s Guide — The System Administrator’s Guide for Red Hat Enterprise Linux 7 documents relevant information regarding the deployment, configuration, and administration of Red Hat Enterprise Linux 7.
Chapter 18. Contacting Global Support Services
Unless you have a Self-Support subscription, when both the Red Hat Documentation website and Customer Portal fail to provide the answers to your questions, you can contact Global Support Services (GSS).
18.1. Gathering Required Information
Several items of information should be gathered before contacting GSS.
Background Information
Ensure you have the following background information at hand before calling GSS:
- Hardware type, make, and model on which the product runs
- Software version
- Latest upgrades
- Any recent changes to the system
- An explanation of the problem and the symptoms
- Any messages or significant information about the issue
If you ever forget your Red Hat login information, it can be recovered at https://access.redhat.com/site/help/LoginAssistance.html.
Diagnostics
The diagnostics report for Red Hat Enterprise Linux is required as well. This report is also known as a sosreport and the program to create the report is provided by the sos package. To install the sos package and all its dependencies on your system:
# yum install sos
To generate the report:
# sosreport
For more information, access the Knowledgebase article at https://access.redhat.com/kb/docs/DOC-3593.
Account and Contact Information
In order to help you, GSS requires your account information to customize their support, as well contact information to get back to you. When you contact GSS ensure you have your:
- Red Hat customer number or Red Hat Network (RHN) login name
- Company name
- Contact name
- Preferred method of contact (phone or email) and contact information (phone number or email address)
Issue Severity
Determining an issue’s severity is important to allow the GSS team to prioritize their work. There are four levels of severity.
- Severity 1 (urgent)
- A problem that severely impacts your use of the software for production purposes. It halts your business operations and has no procedural workaround.
- Severity 2 (high)
- A problem where the software is functioning, but production is severely reduced. It causes a high impact to business operations, and no workaround exists.
- Severity 3 (medium)
- A problem that involves partial, non-critical loss of the use of the software. There is a medium to low impact on your business, and business continues to function by utilizing a workaround.
- Severity 4 (low)
- A general usage question, report of a documentation error, or a recommendation for a future product improvement.
For more information on determining the severity level of an issue, see https://access.redhat.com/support/policy/severity.
Once the issue severity has been determined, submit a service request through the Customer Portal under the Connect
option, or at https://access.redhat.com/support/contact/technicalSupport.html. Note that you need your Red Hat login details in order to submit service requests.
If the severity is level 1 or 2, then follow up your service request with a phone call. Contact information and business hours are found at https://access.redhat.com/support/contact/technicalSupport.html.
If you have a premium subscription, then after hours support is available for Severity 1 and 2 cases.
Turn-around rates for both premium subscriptions and standard subscription can be found at https://access.redhat.com/support/offerings/production/sla.
18.2. Escalating an Issue
If you feel an issue is not being handled correctly or adequately, you can escalate it. There are two types of escalations:
- Technical escalation
- If an issue is not being resolved appropriately or if you need a more senior resource to attend to it.
- Management escalation
- If the issue has become more severe or you believe it requires a higher priority.
More information on escalation, including contacts, is available at https://access.redhat.com/support/escalation.
18.3. Re-opening a Service Request
If there is more relevant information regarding a closed service request (such as the problem reoccurring), you can re-open the request via the Red Hat Customer Portal at https://access.redhat.com/support/policy/mgt_escalation.html or by calling your local support center, the details of which can be found at https://access.redhat.com/support/contact/technicalSupport.html.
In order to re-open a service request, you need the original service-request number.
18.4. Additional Resources
For more information, see the resources listed below.
Online Documentation
- Getting Started — The Getting Started page serves as a starting point for people who purchased a Red Hat subscription and offers the Red Hat Welcome Kit and the Quick Guide to Red Hat Support for download.
- How can a RHEL Self-Support subscription be used? — A Knowledgebase article for customers with a Self-Support subscription.
- Red Hat Global Support Services and public mailing lists — A Knowledgebase article that answers frequent questions about public Red Hat mailing lists.
Appendix A. Changes in Version 12.0
The following sections document features and compatibility changes introduced with Red Hat Developer Toolset 12.1. The list is not full and will be updated.
A.1. Changes in GCC
Red Hat Developer Toolset 12.1 is distributed with GCC 12.2.1.
The following features have been added or modified since the previous release of Red Hat Developer Toolset:
General Improvements
-
Vectorization is enabled at
-O2
, which is now equivalent to the original-O2 -ftree-vectorize -fvect-cost-model=very-cheap
.
Language-specific Improvements
OpenMP
-
OpenMP 5.0 support has been extended. The
close map
modifier and theaffinity
clause are now supported. -
Several newly implemented OpenMP 5.1 features have been added. For example, support for expressing OpenMP directives as C++ 11 attributes, the
masked
andscope
construct, thenothing
anderror
directives, usingprimary
with theproc_bind
clause andOMP_PROC_BIND
environment variable, thereproducible
andunconstrained
modifiers to theorder
clause, and, for C and C++ only, thealign
andallocator
modifiers to theallocate
clause, and the atomic extensions.
C family
New features and attributes:
-
Support for the
__builtin_shufflevector
built-in compatible with the clang language extension. -
Support for the
unavailable
attribute. -
A new built-in function,
__builtin_assoc_barrier
, used to inhibit re-association of floating-point expressions. -
Support for the
__builtin_dynamic_object_size
built-in compatible with the clang language extension.
-
Support for the
New warnings:
-
-Wbidi-chars
warns about potentially misleading UTF-8 bidirectional control characters. The default is-Wbidi-chars=unpaired
. -
-Warray-compare
warns about comparisons between two operands of array type.
-
Enhanced warnings:
-
-Wattributes
has been extended, so it is now possible to use-Wno-attributes=ns::attr
or-Wno-attributes=ns::
to suppress warnings about unknown scoped attributes in C++11 and C2X. Similarly, the#pragma
GCC diagnosticignored_attributes "vendor::attr"
can be used to do the same thing.
-
C
- Digit separators, like in C++, are supported for C2X.
-
The
#elifdef
and#elifndef
preprocessing directives are now supported. -
The
printf
andscanf
formats checking with-Wformat
now support the%b
format specified by C2X for binary integers, and the%B
format recommended by C2X forprintf
.
C++
The following C++23 features have been implemented:
-
P1938R3: Implement
if consteval
-
P0849R8:
auto(x)
:decay-copy
in the language -
P2242R3: Non-literal variables (and labels and gotos) in
constexpr
functions -
P2334R1: Support for preprocessing directives
elifdef
andelifndef
-
P2360R0: Extend
init-statement
to allowalias-declaration
- P2128R6: Multidimensional subscript operator
- DR 2397: auto specifier for pointers and references to arrays
-
P1938R3: Implement
-
A new command-line option,
-fimplicit-constexpr
, used to make inline functions implicitlyconstexpr
. -
A new command-line option,
-ffold-simple-inlines
, used to fold calls to certain trivial inline functions such asstd::move
,std::forward
,std::addressof
, andstd::as_const
. - Deduction guides can be declared at class scope
-
-Wuninitialized
now warns about using uninitialized variables in member initializer lists. New warnings:
-
New warning options for the following C++ language mismatches:
-Wc11-extensions`, `-Wc14-extensions
,-Wc17-extensions`, `-Wc20-extensions
, and-Wc++23-extensions
. They are enabled by default and are used to control existing pedwarns about occurrences of new C++ constructs in code using an old C++ standard dialect. -
A new warning,
-Wmissing-requires
, warns about missingrequires
. -
The existing
std::is_constant_evaluated
warning is extended to warn in more cases.
-
New warning options for the following C++ language mismatches:
For more information about new C++ features in Red Hat Developer Toolset 12.1, see the following Red Hat Developers article.
Runtime library libstdC++
The following experimental C++20 support features have been improved:
-
std::vector
,std::basic_string
,std::optional
, andstd::variant
can now be used inconstexpr
functions. -
std::make_shared
for arrays with default initialization, andstd::atomic<std::shared_ptr<T>>
. - Layout-compatibility and pointer-interconvertibility traits.
-
The following experimental C++23 support features have been improved:
-
Monadic operations for
std::optional
. -
std::move_only_function
-
<spanstream>
-
std::basic_string::resize_and_overwrite
-
std::unique_ptr
can now be used inconstexpr
functions. -
<stacktrace>
(not built by default, requires linking to an extra library). -
<stdatomic.h>
-
std::invoke_r
-
constexpr
std::type_info::operator==
-
Monadic operations for
Architecture-specific Improvements
The 64-bit ARM architecture
-
A number of new CPUs are supported through the
-mcpu
and-mtune
options. -
The 64-byte atomic load/store intrinsics to accelerator memory from the 2020 Arm Architecture extensions are supported through the
+ls64
option extension. -
Initial code generation support is supported for hardware instructions that accelerate the
memcpy
,memmove
, andmemset
standard functions. Generate these instructions when compiling with the+mopsoption
extension. -
The Arm C Language Extensions (ACLE) Advanced Single Instruction Multiple Data (SIMD) intrinsics accessible through the
arm_neon.h
header are significantly reimplemented and generate higher-performing code than previous GCC versions.
AMD and Intel 64-bit architectures
-
New ISA extension support for Intel AVX512-FP16 was added. AVX512FP16 intrinsics are available via the
-mavx512fp16
compiler switch. -
For both C and C++, the
_Float16 type
is supported on systems withSSE2
enabled. -
Mitigation against straight line speculation (SLS) for function return and indirect jump is supported via
-mharden-sls=[none|all|return|indirect-jmp]
.
A.2. Changes in elfutils
Red Hat Developer Toolset 12.1 is distributed with elfutils 0.187.
The following features have been added or modified since the previous release of Red Hat Developer Toolset:
-
Support for the NVIDIA Cuda line map extensions in the
libdw
library. -
The
eu-addr2line
executable now defaults to the-A
,--absolute
option, which shows file names including the full compilation directory. Use the new--relative
option to revert to the old behavior. -
The
eu-readelf
andeu-elflint
executables now recognize FDO Packaging Metadata ELF notes. The
debuginfod
executable now supports:-
A new
-d :memory:
option for in-memory databases. -
A new
-r
option to use-I
or-X
regexes for grooming stale files. -
A new
-C
option for connection thread pooling. -
A new
--passive
mode for serving from read-only databases.
-
A new
-
The
debuginfod-client
directory now supports setting theDEBUGINFOD_MAXSIZE
,DEBUGINFOD_MAXTIME
, andDEBUGINFOD_RETRY
environment variables. Negative cache files are now zero-sized, which work better than no-permission files when scanning files or making backups.
A.3. Changes in GDB
Red Hat Developer Toolset 12.1 is distributed with GDB 11.2.
The following features have been added or modified since the previous release of Red Hat Developer Toolset:
New features
- New support for Aarch64 MTE. See new commands with the "memory-tag" prefix.
--qualified
option for-break-insert
and-dprintf-insert
. This option looks for an exact match of the user’s event location instead of searching in all scopes.For example,
break --qualified foo
will look for a symbol named foo in the global scope. Without--qualified
, GDB will search all scopes for a symbol with that name.-
--force-condition
: Any supplied condition is defined even if it is currently invalid. -
-break-condition --force
: Likewise for the MI command. -
-file-list-exec-source-files
accepts optionalREGEXP
to limit output. .gdbinit
search path includes the config directory. The order is:- $XDG_CONFIG_HOME/gdb/gdbinit
- $HOME/.config/gdb/gdbinit
- $HOME/.gdbinit.
-
Support for
~/.config/gdb/gdbearlyinit
or~/.gdbearlyinit
. -
-eix
and-eiex
early initialization file options.
Terminal user interface (TUI)
- Support for mouse actions inside terminal user interface (TUI) windows.
- Key combinations that do not act on the focused window are now passed to GDB.
New and improved commands
-
A new
show print memory-tag-violations
command. -
A new
set print memory-tag-violations
command. -
A new
memory-tag show-logical-tag
command. -
A new
memory-tag with-logical-tag
command. -
A new
memory-tag show-allocation-tag
command. -
A new
memory-tag check
command. -
New
show startup-quietly
andset startup-quietly
commands: A way to specify-q
or-quiet
in GDB scripts. Only valid in early initialization files. -
New
show print type hex
andset print type hex
commands: Tells GDB to print sizes or offsets for structure members in hexidecimal instead of decimal. -
New
show python ignore-environment
andset python ignore-environment
commands: If enabled, GDB’s Python interpreter ignores Python environment variables, much like passing-E
to the Python executable. Only valid in early initialization files. -
New
show python dont-write-bytecode
andset python dont-write-bytecode
commands: If 'off', these commands suppress GDB’s Python interpreter from writing bytecode compiled objects of imported modules, much like passing-B
to the Python executable. Only valid in early initialization files. -
break LOCATION if CONDITION
: If CONDITION is invalid, GDB refuses to set a breakpoint. The-force-condition
option overrides this. -
CONDITION -force N COND
: Same as the previous command. -
inferior [ID]
: When ID is omitted, this command prints information about the current inferior. Otherwise, unchanged. -
ptype[/FLAGS] TYPE | EXPRESSION
: Use the '/x' flag to use hexidecimal notation when printing sizes and offsets of struct members. Use the '/d' flag to do the same but using decimal. -
info sources
: Output has been restructured.
Python API
-
Inferior objects contain a read-only
connection_num
attribute. -
New
gdb.Frame.level()
method. -
New
gdb.PendingFrame.level()
method. -
gdb.BreakpoiontEvent
emitted instead ofgdb.Stop
.
A.4. Changes in strace
Red Hat Developer Toolset 12.1 is distributed with strace 5.18.
The following features have been added or modified since the previous release of Red Hat Developer Toolset:
Changes in Behavior
Modified
%process
class contains system calls associated with process lifecycle (creation, execution, and termination):-
New calls:
kill
,tkill
,tgkill
,pidfd_send_signal
, andrt_sigqueueinfo
-
Removed calls:
arch_prctl
andunshare
-
New calls:
Improvements
-
A new
--secontext=mismatch
option finds mismatches in SELinux contexts. -
A new
--strings-in-hex=non-ascii-chars
option for using hexadecimal numbers instead of octal characters in escape sequences in the output strings. -
A new
--decode-pids=comm
option, and its alias-Y
, print command names for PIDs. -
A new
--decode-pids=pidns
alias to the--pidns-translation
option. -
Printing the current working directory when the
AT_FDCWD
constant is used with the--decode-fds=path
option enabled is implemented. -
A new
--tips
option printsstrace
tips, tricks, and tweaks at the end of a tracing session. -
Extended personality designation syntax of system call specification expressions to support
all@pers
and%class@pers
. - Enhanced rejection of invalid system call numbers in syscall specification expressions.
-
Decoding of the following system calls is implemented:
futex_waitv
,memfd_secret
,process_mrelease
,quotactl_fd
, andset_mempolicy_home_node
. -
Decoding of the following system calls is enhanced:
bpf
,io_uring_register
,prctl
,seccomp
, andtimes
. -
Decoding of the following
ioctl
commands is implemented:COUNTER_*
,HDIO_
,KD*
,LIRC*
,RTC_PARAM_GET
,RTC_PARAM_SET
, andSECCOMP_*
. -
Decoding of the
BTRFS_IOC_FS_INFO
ioctl
command is enhanced. -
Decoding of the following netlink messages is implemented:
RTM_NEWCACHEREPORT
,RTM_{NEW,DEL,GET}NEXTHOP
, andRTM_{NEW,GET}STATS NETLINK_ROUTE
. -
Decoding of the following netlink attributes is enhanced:
IFLA_*
,MDBA_ROUTER_PATTR_*
,TCA_ACT_IN_HW_COUNT
,*_INTVL
, and*_TIMER
. -
Decoding of the
siginfo_t.si_pkey
field is implemented. -
Printing system call names in places where the associated
AUDIT_ARCH_*
value is present (the ptracePTRACE_GET_SYSCALL_INFO
request,SIGSYS
siginfo_t
) is improved. -
Decoding of the following socket addresses is implemented:
AF_ALG
,AF_IEEE802154
,AF_MCTP
,AF_NFC
,AF_QIPCRTR
,AF_RRPC
,AF_VSOCK
, andAF_XDP
. -
Decoding of the
AF_IPX
andAF_NETLINK
socket addresses is enhanced. -
Lists of the following constants are updated:
AF_*
,ARPHRD_*
,AUDIT_*
,BPF_*
,BR_*
,BTRFS_*
,DEVCONF_*
,DM_*
,ETH_P_*
,FAN_*
,FAN_REPORT_*
,IFA_*
,IFLA_*
,IORING_*
,IOSQE_*
,IPV4_DEVCONF_*
,KEY_*
,KVM_*
,MADV_*
,MODULE_INIT_*
,MOUNT_ATTR_*
,MOVE_MOUNT_*
,MPOL_*
,NDA_*
,PACKET_*
,RTM_*
,SCTP_*
,SO_*
,TCA_ACT_*
,UFFD_*
,V4L2_*
,XFRM_MSG_*
, and*_MAGIC
. -
Lists of
ioctl
commands are updated to match the Linux 5.18 kernel.
Bug Fixes
-
Printing of the updated value of
union bpf_attr.next_id
on the exiting ofbpf(BPF_*_GET_NEXT_ID)
calls is fixed. -
Printing of the
struct bpf_prog_info.map_ids
array is fixed. -
The
dev
,pidfd
, andsocket
arguments of the--print-fds
option no longer imply thepath
argument.
A.5. Changes in SystemTap
Red Hat Developer Toolset 12.1 is distributed with SystemTap 4.7.
The following features have been added or modified since the previous release of Red Hat Developer Toolset:
-
A new
--sign-module
option to manually sign modules with a MOK key, for use on SecureBoot systems. -
A new
stap-profile-annotate
tool to produce system-wide profiles of annotated source code. - A new general Python tapset for probing function entry and return.
-
Extended
$foo$
processing for kernel-space probes for strings that may be in user-space. - Extended the regular-expression language for non-capturing groups.
- Added tapset support for several recently added kernel system calls.
For further information about notable changes, see the upstream SystemTap 4.7 release notes.
A.6. Changes in Dyninst
Red Hat Developer Toolset 12.1 is distributed with Dyninst 12.1.0.
The following features have been added since the previous release of Red Hat Developer Toolset 12.1:
-
Initial support for
glibc-2.35
multiple namespaces - Concurrency fixes for DWARF parallel parsing
-
Better support for the
CUDA
andCDNA2
GPU binaries - Better support for IBM POWER Systems (little endian) register access
- Better support for PIE binaries
- Corrected parsing for catch blocks
-
Corrected access to 64-bit Arm (
aarch64
) floating point registers
A.7. Changes in Annobin
Red Hat Developer Toolset 12.1 is distributed with Annobin 11.08.
The following features have been added or modified since the previous release of Red Hat Developer Toolset:
-
A new command line option for annocheck tells it to avoid using the
debuginfod
service, if it is unable to find debug information in another way. Usingdebuginfod
provides annocheck with more information, but it can also cause significant slow downs in annocheck’s performance if thedebuginfod
server is unavailable. -
The Annobin sources can now be built using
meson
andninja
rather than configure and make if desired. - Annocheck now supports binaries built by the Rust 1.18 compiler.
Appendix B. Changes in Version 12.1
The following sections document features and bug fixes introduced in Red Hat Developer Toolset 12.1.
B.1. Changes in GCC
GCC in Red Hat Developer Toolset 12.1 has been updated to GCC 12.2.1, which provides many bug fixes and enhancements that are available in upstream GCC.
B.2. Changes in Annobin
Annobin in Red Hat Developer Toolset 12.1 has been updated to Annobin 11.08.
B.3. Changes in binutils
With the release of Red Hat Developer Toolset 12.1, a security update is available for binutils 2.36.1.