宿主机kernel识别kvm-vcpu线程的一种方法

设想

qemu会探入kvm内核，可否有kvm自己来将vcpu线程进行标识，这样调度器就可以根据标识来识别kvm的vcpu线程。

代码

task_struct增加成员

struct task_struct {...unsigned int kvm_thread;...
}

kvm_thread默认赋值

/*头文件增加定义*/
#define NO_KVM_THREAD   0
#define KVM_VCPU        1
#define KVM_THREAD      2/*init_task中初始化，init/init_task.c*/
.kvm_thread = NO_KVM_THREAD,/*fork创建新进程初始化，kernel/fork.c, copy_process()函数*/
p->kvm_thread = NO_KVM_THREAD;

VCPU线程修改kvm_thread

/*virt/kvm/kvm_main.c中kvm_vm_ioctl_create_vcpu()函数*/
current->kvm_thread = KVM_VCPU

CFS调度器判断VCPU线程

/*kernel/sched/fair.c中__enqueue_entity()函数*/
if(entity_is_task(se)) {if(task_of(se)->kvm_thread == KVM_VCPU) {se->vruntime >>= 1;}
}

验证

运行qemu虚拟机ubuntu，在ubuntu中替换内核，并再运行qemu虚拟机（需要-enable-kvm)。

跑一个双核的qemu虚拟机，然后看预留的打印：

用htop命令查看具体线程和pid：

用top看cpu使用率：

问题

目前没看出vruntime减半带来的具体的效应。不过应该可以通过该方法来让调度器识别kvm的vcpu线程。

遇到的问题记录下：

qemu虚拟机起来了，但kvm标识vcpu线程代码未起作用

qemu命令需要-enable-kvm，否则不会使用kvm内核模块。
嵌套qemu中，虚拟机ubuntu提示kvm：no hardware support

qemu命令中需要-cpu kvm64,+vmx来支持硬件虚拟化嵌套。
只识别了vcpu线程，其他qemu线程如何识别？不同qemu虚拟机的线程可否区分？

待继续分析完善。

宿主机kernel识别kvm-vcpu线程的一种方法相关推荐

java创建线程的两种方法区别
在Java中创建一个线程有两种方法:继承Thread类和实现Runnable接口. 下面通过两个例子来分析两者的区别: 1)继承Thread类 public class TestThread exte ...
【 Thread】创建线程的2种方法
(一)Thread类 1.结构 java.lang.Object |---java.lang.Thread 2.创建线程的两种方法 (1)一种方法是将类声明为Thread的子类,该子类应重写Threa ...
Java学习笔记：创建线程的两种方法
Java学习笔记:创建线程的两种方法一.预备工作 1.创建Maven项目ThreadDemo 2.在pom.xml里添加依赖二.继承Thread类创建子线程
多线程之终止线程的四种方法
终止线程的四种方法第一种:正常运行结束第二种:使用退出标志退出线程第三种:interrupt()方法退出第四种:stop方法退出第一种:正常运行结束这种就是程序正常执行完run方法或者ce ...
java 终止方法_Java中终止线程的三种方法
Java中终止线程的三种方法 Thread.stop, Thread.suspend, Thread.resume 和Runtime.runFinalizersOnExit 这些终止线程运行的方法已经 ...
Java创建线程的三种方法
这里不会贴代码,只是将创建线程的三种方法做个笼统的介绍,再根据源码添加上自己的分析. 通过三种方法可以创建java线程: 1.继承Thread类. 2.实现Runnable接口. 3.实现Callab ...
Java 创建线程的三种方法比较
在学习编程的过程中,我觉得不止要获得课本的知识,更多的是通过学习技术知识提高解决问题的能力,这样我们才能走在最前方,本文主要讲述Java 创建线程的三种方法比较, 更多Java专业知识,广州疯狂jav ...
TIL：创建Java线程的两种方法
Java最强大的功能之一是它允许人们轻松管理线程以执行程序中的各种任务. 正确使用线程可以提高程序的效率. 也就是说,今天我了解了创建这些线程的两种方法: 第一种方法:实现可运行 Runnable是抽 ...
OMP 设置线程的3种方法
设置线程的3种方法 1. 在子语句 data clause 中设置 : num_threads( ) #pragma omp parallel for default(none) shared(x) ...

宿主机kernel识别kvm-vcpu线程的一种方法

设想

代码

验证

问题

宿主机kernel识别kvm-vcpu线程的一种方法相关推荐

最新文章

热门文章