<Linux>Linux内核启动分析(二)——start_kernel

在前一篇对head.S的分析中,我们知道内核启动的第一阶段的是处理u-boot传进来的机器id,由此来判断内核是否支持这个CPU以及该单板。而head.S最后跳到start_kernel这函数中作进一步的处理。分析如下:

一、start_kernel

在start_kernel这个函数中首先进行一系列的初始化,咱们就先不去具体分析每一个初始化函数,主要看最后两行的的setup_arch和 setupc_command_line这两个函数。在前面分析中,我们知道head.S利用u-boot传入的机器ID来判断内核和开发板的关系,而u-boot同时还传入了另外一些参数。在start_kernel,正是利用最后两行的两个函数来处理其他传入的参数。

二、setup_arch


我们跟踪setup_arch这个函数,在783行的这个判断不就是前面分析的u-boot启动内核的时候thekernel传入的第二个参数吗?定义如下:

theKernel (0, bd->bi_arch_number, bd->bi_boot_params);而接下来对每个tag的解析,(若有兴趣,请参考原文:http://blog.csdn.net/stephen_lu_fahai/article/details/70146059)正是在那篇博文中列的图:


也就是setup_arch这个函数对这些传入的参数做解析并且保存(我还没去看具体是如何实现的安静,它是调用parse_tags这个函数进行解析的)。

三、setup_command_line

需要注意的是,在811行,parse_comline函数是单独处理的,对应上图“一个字符串”区域。之所以会单独处理命令行,是因为命令行很重要。我们看到它有两个参数cmdline_p, 以及from;而from的定义为:char *from = default_command_line;,也就是说,如果有命令传入,就解析传入的命令,如果没有,就使用默认的命令。我们进入看一下:


这个函数要做的事情把命令保存到command_line这个数组,以便以后使用。

四、挂接根文件系统

我们在前面一片博文就说过,启动内核的目的是为了执行应用程序,而要执行应用程序就得先挂接到根文件系统。下面是其流程:

start_kernel进行一系列的初始化和对u-boot传入的参数和命令进行处理之后,在最后会跳到rest_init();这个函数。我们来看一下这个函数要做什么事情


431行,创建一个内核线程,我们姑且可以看做是调用kernel_init这个函数,继续跟踪kernel_init:


继续跟踪prepare_namespace:


到这来我们发现,调用mout_root挂接到根文件系统。

小结一下挂接到根文件系统的调用流程:

start_kernel—>rest_init—>prepare_namespace—>mout_root

四、执行用户程序

那么挂接到根文件系统之后要做什么事情?接着往下:

kernel_init函数最后要执行的是init_post这个函数:


我们进去看一下:


756行,打开dev\console目录

779~782执行用户程序。

最后总结一下内核的启动流程吧:(缩进表示调用关系)

  • 0
    点赞
  • 4
    收藏
    觉得还不错? 一键收藏
  • 0
    评论
kernel<<<>>>用法是指在CUDA编程中,使用<<<>>>符号来定义并行执行的内核函数。内核函数是在GPU上执行的函数,每个线程都会执行一次该函数。<<<>>>符号中的参数表示线程块(block)和线程(thread)的数量。例如,kernel<<<block, thread>>>()表示在block个线程块中,每个线程块中有thread个线程。 在上述示例中,kernel2和kernel3是两个并行执行的内核函数,<<<grid, block>>>表示在grid个线程块中,每个线程块中有block个线程。这样就可以同时启动多个线程块执行相同的内核函数。 在CUDA编程中,还可以使用__syncthreads()函数来同步线程。这个函数会让所有的线程在同一点等待,直到所有线程都执行到这个点。这可以用来确保线程之间的同步和协作。 另外,在示例中的cudaMemcpy()函数用于在主机和设备之间进行内存的数据传输。该函数的参数包括目标内存地址、源内存地址、数据数量和传输方向。例如,cudaMemcpy(dst, src, count, cudaMemcpyKind)表示将count个数据从src内存地址复制到dst内存地址。 综上所述,kernel<<<>>>用法是在CUDA编程中定义并行执行的内核函数,通过设置线程块和线程的数量来控制并发执行的规模。同时可以使用__syncthreads()函数来同步线程,以及使用cudaMemcpy()函数来进行主机和设备之间的数据传输。<span class="em">1</span><span class="em">2</span><span class="em">3</span> #### 引用[.reference_title] - *1* *2* *3* [「并行学习」CUDA](https://blog.csdn.net/weixin_41468462/article/details/103378541)[target="_blank" data-report-click={"spm":"1018.2226.3001.9630","extra":{"utm_source":"vip_chatgpt_common_search_pc_result","utm_medium":"distribute.pc_search_result.none-task-cask-2~all~insert_cask~default-1-null.142^v93^chatsearchT3_1"}}] [.reference_item style="max-width: 100%"] [ .reference_list ]

“相关推荐”对你有帮助么?

  • 非常没帮助
  • 没帮助
  • 一般
  • 有帮助
  • 非常有帮助
提交
评论
添加红包

请填写红包祝福语或标题

红包个数最小为10个

红包金额最低5元

当前余额3.43前往充值 >
需支付:10.00
成就一亿技术人!
领取后你会自动成为博主和红包主的粉丝 规则
hope_wisdom
发出的红包
实付
使用余额支付
点击重新获取
扫码支付
钱包余额 0

抵扣说明:

1.余额是钱包充值的虚拟货币,按照1:1的比例进行支付金额的抵扣。
2.余额无法直接购买下载,可以购买VIP、付费专栏及课程。

余额充值