环境

Centos 6.4 x86_64

oprofile-0.9.9

oprofile安装

#wget http://ncu.dl.sourceforge.net/project/oprofile/oprofile/oprofile-0.9.9/oprofile-0.9.9.tar.gz

#tar -zxvf oprofile-0.9.9.tar.gz

#cd oprofile-0.9.9

#./configure

#make

#make install

oprofile使用

常用命令：

使用oprofile检测CPU，需要经过初始化、启动、导出数据、查看结果四个步骤。

初始化

opcontrol --no-vmlinux : oprofile启动后，不记录内核模块、内核代码相关统计数据

opcontrol --init : 加载oprofile模块、oprofile驱动程序

oprofile控制

opcontrol --start : 指示oprofile启动检测

opcontrol --dump : 指示将oprofile检测到的数据写入文件

opcontrol --reset : 清空之前检测的数据记录

opcontrol --h : 关闭oprofile进程

查看结果

opreport :默认查看oprofile检测结果

opreport -l : 以函数的角度显示检测结果

opreport -l oprofile_test : 以函数的角度，针对oprofile_test进程显示检测结果

opannotate -s oprofile_test : 以代码的角度，针对oprofile_test进程显示检测结果

opannotate -s /lib64/libc-2.12.so : 以代码的角度，针对libc-2.4.so库显示检测结果

在oprofile安装完成后，第一步初始化oprofile

[root@compute oprofile-0.9.9]# opcontrol --init

而后启动oprofile

[root@compute oprofile-0.9.9]# opcontrol --start --no-vmlinux

ATTENTION: Use of opcontrol is discouraged.  Please see the man page for operf.

Using default event: CPU_CLK_UNHALTED:100000:0:1:1

Using 2.6+ OProfile kernel interface.

Using log file /var/lib/oprofile/samples/oprofiled.log

Daemon started.

Profiler running.

通过默认的方式查看CPU检测报告

[root@compute oprofile-0.9.9]# opreport | less

Using /var/lib/oprofile/samples/ for samples directory.

CPU: Intel Westmere microarchitecture, speed 2393.96 MHz (estimated)

Counted CPU_CLK_UNHALTED events (Clock cycles when not halted) with a unit mask of 0x00 (No unit mask) count 100000

CPU_CLK_UNHALT...|

  samples|      %|

------------------

   361031 83.4576 vmlinux

    32789  7.5797 ext4

    14667  3.3905 jbd2

    10162  2.3491 no-vmlinux

     3178  0.7346 libc-2.12.so

     1798  0.4156 mptbase

     1386  0.3204 oprofiled

     1380  0.3190 oprofile

     1267  0.2929 opannotate

     1242  0.2871 libpython2.6.so.1.0

     1102  0.2547 mptscsih

      924  0.2136 bash

      290  0.0670 ld-2.12.so

      201  0.0465 kvm

      159  0.0368 bnx2

      159  0.0368 libstdc++.so.6.0.13

      120  0.0277 sd_mod

通过函数方式显示检测结果

[root@compute oprofile-0.9.9]# opreport -l | less

CPU: Intel Westmere microarchitecture, speed 2393.96 MHz (estimated)

Counted CPU_CLK_UNHALTED events (Clock cycles when not halted) with a unit mask of 0x00 (No unit mask) count 100000

samples  %        image name               app name                 symbol name

107138   20.1679  no-vmlinux               no-vmlinux               /no-vmlinux

51905     9.7707  vmlinux                  vmlinux                  intel_idle

32789     6.1723  ext4                     ext4                     /ext4

32755     6.1659  vmlinux                  vmlinux                  port_inb

21769     4.0978  vmlinux                  vmlinux                  copy_user_generic_string

16469     3.1002  vmlinux                  vmlinux                  __clear_user

14667     2.7609  jbd2                     jbd2                     /jbd2

13871     2.6111  vmlinux                  vmlinux                  native_sched_clock

8691      1.6360  vmlinux                  vmlinux                  get_page_from_freelist

5864      1.1039  vmlinux                  vmlinux                  find_busiest_group

5701      1.0732  vmlinux                  vmlinux                  mark_page_accessed

2894      0.5448  vmlinux                  vmlinux                  __schedule

2888      0.5436  vmlinux                  vmlinux                  __list_del_entry

2817      0.5303  vmlinux                  vmlinux                  menu_select

2772      0.5218  vmlinux                  vmlinux                  kmem_cache_alloc

2652      0.4992  vmlinux                  vmlinux                  __alloc_pages_slowpath

2478      0.4665  vmlinux                  vmlinux                  __wake_up_bit

2438      0.4589  vmlinux                  vmlinux                  __hrtimer_start_range_ns

2428      0.4571  vmlinux                  vmlinux                  kmem_cache_free

2262      0.4258  vmlinux                  vmlinux                  __list_add

下同编写简单代码消耗CPU，通过opannotate来了解CPU的占用情况，代码如下：

#vi test.c

int main()

{

        int a = 0, b = 0;

        for (; a < 1000000000; a++  )

                {

                        b++;

                }

}

#gcc -o oprofile_test test.c

执行该代码

#./oprofile_test &

将检测数据写入文件

#opcontrol --dump

查看该代码的CPU检测数据

[root@compute ~]# opreport -l oprofile_test

Using /var/lib/oprofile/samples/ for samples directory.

CPU: Intel Westmere microarchitecture, speed 2393.96 MHz (estimated)

Counted CPU_CLK_UNHALTED events (Clock cycles when not halted) with a unit mask of 0x00 (No unit mask) count 100000

samples  %        symbol name

492407   100.000  main

通过opannotate查看代码层CPU的占用情况

[root@compute ~]# opannotate -s oprofile_test

Using /var/lib/oprofile/samples/ for session-dir

/*

 * Command line: opannotate -s oprofile_test

 *

 * Interpretation of command line:

 * Output annotated source file with samples

 * Output all files

 *

 * CPU: Intel Westmere microarchitecture, speed 2393.96 MHz (estimated)

 * Counted CPU_CLK_UNHALTED events (Clock cycles when not halted) with a unit mask of 0x00 (No unit mask) count 100000

 */

/*

 * Total samples for file : "/root/test.c"

 *

 * 492407 100.000

 */

               :int main()

               :{ /* main total: 492407 100.000 */

               :        int a = 0, b = 0;

343285 69.7157 :        for (; a < 1000000000; a++  )

               :                {

149122 30.2843 :                        b++;

               :                }

               :}