• <tr id="yyy80"></tr>
  • <sup id="yyy80"></sup>
  • <tfoot id="yyy80"><noscript id="yyy80"></noscript></tfoot>
  • 99热精品在线国产_美女午夜性视频免费_国产精品国产高清国产av_av欧美777_自拍偷自拍亚洲精品老妇_亚洲熟女精品中文字幕_www日本黄色视频网_国产精品野战在线观看 ?

    GPU圖像并行處理設(shè)計模型研究*

    2016-12-13 02:06:59全吉成王宏偉
    艦船電子工程 2016年11期
    關(guān)鍵詞:并行算法線程圖像處理

    王 平 全吉成 王宏偉

    (空軍航空大學航空航天情報系 長春 130022)

    ?

    GPU圖像并行處理設(shè)計模型研究*

    王 平 全吉成 王宏偉

    (空軍航空大學航空航天情報系 長春 130022)

    GPU通用計算的發(fā)展為圖像處理提供了新的技術(shù)手段,目前一些圖像處理算法已經(jīng)移植到GPU中且得到了較好的加速效果,但是并沒有形成通用的并行設(shè)計模型,推廣性差。為此,論文在研究GPU結(jié)構(gòu)特點以及已有的GPU圖像處理并行算法的基礎(chǔ)上,提出了單GPU和多GPU圖像并行處理設(shè)計模型,并通過圖像平滑并行算法在GPU中的執(zhí)行驗證了該模型的有效性。試驗結(jié)果表明,該模型在GPU圖像處理中通用性較好,為更多算法的并行化處理提供了理論借鑒。

    圖像算法; 并行化; GPU; 模型; 通用性

    Class Number TN911

    1 引言

    隨著圖像獲取手段的發(fā)展,獲取圖像的效率逐漸加快以及圖像分辨率急劇增長,現(xiàn)有的圖像處理工具已經(jīng)無法滿足海量圖像數(shù)據(jù)的快速處理,造成影像數(shù)據(jù)的大量堆積。因此如何快速、高效地進行海量圖像數(shù)據(jù)處理是圖像處理領(lǐng)域亟待解決的問題。

    圖形處理器(Graphic Process Unit,GPU)在通用計算方面取得了快速發(fā)展,計算能力已經(jīng)遠遠超過了CPU,成為實現(xiàn)高性能計算的重要部件[1]。近年來,不少專家學者將圖像處理算法移植到GPU中[2~5],并取得了很高的算法加速比,加快了圖像算法并行化處理的發(fā)展。這些映射到GPU中算法只是一些特定的算法,并沒有形成通用的GPU圖像處理并行設(shè)計模型,難以推廣到其他的圖像處理算法中。

    本文根據(jù)GPU體系結(jié)構(gòu)的特點以及對已有的GPU圖像處理并行算法的分析,提出了通用的GPU圖像并行處理設(shè)計模型,并通過圖像平滑算法進行GPU并行處理來驗證模型的有效性,進而可以將模型擴展到更多圖像處理算法中。

    2 GPU圖像并行處理設(shè)計模型

    GPU圖像處理并行設(shè)計模型主要描述圖像串行算法進行GPU并行處理的一般性的解決方案。 這樣可以讓我們復(fù)用已經(jīng)建立的設(shè)計模型,為自己的算法并行化問題找到有效的解決方法。在大量圖像處理算法并行化分析的基礎(chǔ)上,本文提出的針對單個GPU的通用的GPU圖像處理并行設(shè)計模型包括以下四個步驟:串行算法的并行化分析,并行粒度劃分,映射到GPU中,程序的優(yōu)化,如圖1所示。如果含有多個GPU,并行設(shè)計模型應(yīng)該包括五個步驟:串行算法的并行化分析,任務(wù)劃分,并行粒度劃分,映射到GPU中,程序的優(yōu)化,如圖2所示。

    圖1 GPU圖像并行處理設(shè)計模型

    圖2 GPUs圖像并行處理設(shè)計模型

    1) 串行算法的并行化分析:串行算法的并行化分析就是找尋串行算法中計算量最大、處理時間最耗時、數(shù)據(jù)相關(guān)性小的部分,然后對其進行并行化分析。這主要以下三個方法[6]:

    (1)根據(jù)算法中已有的并行性將算法改變成并行算法;

    (2)從算法本身要處理的問題特征著手把傳統(tǒng)算法并行化;

    (3)根據(jù)已有經(jīng)典并行算法的設(shè)計思路,改造傳統(tǒng)圖像處理算法。

    2) 任務(wù)劃分:在并行算法中,將整個任務(wù)分成若干個子任務(wù),每個GPU對應(yīng)一個子任務(wù)。在多核CPU上啟動多個線程,每個線程控制一個設(shè)備,實現(xiàn)設(shè)備間的并行計算。

    3) 并行粒度劃分:GPU中執(zhí)行的核函數(shù)Kernel可以看做一個線程網(wǎng)格,一個線程網(wǎng)格包含若干個線程塊,每個線程塊包含若干個線程,如圖3所示。在GPU具體執(zhí)行中,線程塊和塊中線程被調(diào)度分別實現(xiàn)粗粒度和細粒度并行[7]。并行粒度劃分就是將圖像并行算法映射到線程塊和塊中的線程中,從而實現(xiàn)GPU內(nèi)粗、細粒度并行執(zhí)行。

    圖3 GPU內(nèi)部線程組織方式

    4) 映射到GPU中:將并行算法映射到GPU眾核的架構(gòu)上,通過多線程并行執(zhí)行來實現(xiàn)算法的并行運行。具體步驟如下:

    (1)分配顯存空間,將影像數(shù)據(jù)從主存?zhèn)鬏數(shù)斤@存中;

    (2)設(shè)置執(zhí)行配置即設(shè)置線程塊大小和數(shù)量,啟動核函數(shù)Kernel;

    (3)將結(jié)果影像數(shù)據(jù)從顯存?zhèn)鬏數(shù)街鞔妗?/p>

    5) 程序優(yōu)化:在以上幾個步驟完成后,程序能夠正確運行,并且結(jié)果驗證準確,這是程序優(yōu)化的前提,也是程序優(yōu)化的起點。程序優(yōu)化包括存儲器優(yōu)化、指令優(yōu)化和編碼優(yōu)化。存儲器優(yōu)化是指優(yōu)化存儲器利用率和最大化全局存儲器吞吐量[8]。指令優(yōu)化是指使用GPU提供的存儲器控制、線程控制等各種優(yōu)化指令,能顯著提升程序的性能。編碼優(yōu)化指程序編寫時,盡可能少用if分支語句;使用#unroll指令展開循環(huán)語句;在保證精度的情況下,盡可能的使用專用的算術(shù)指令等[9~10]??偠灾绦騼?yōu)化的核心思想是改進計算訪存比以及各存儲層次上的延遲隱藏[11]。

    3 并行設(shè)計模型的驗證

    3.1 算法并行化分析

    圖像平滑算法是針對單個像素進行計算,各個像素之間的操作沒有相關(guān)性,而且計算量大,并行程度高,適合移植到GPU中進行并行處理。

    3.2 并行粒度劃分

    平滑后的圖像與GPU線程網(wǎng)格對應(yīng),將圖像進行分塊,使每個圖像塊與一個線程塊對應(yīng),每個圖像分塊中像素與線程塊中的線程相對應(yīng),保證線程塊中線程對每一個像素進行處理。這樣就實現(xiàn)了線程塊之間的在SM中粗粒度并行執(zhí)行,以及線程塊內(nèi)的線程在CUDA核心中細粒度并行執(zhí)行。

    3.3 映射到GPU中

    根據(jù)圖像大小分配顯存大小,將圖像數(shù)據(jù)從主存?zhèn)鬏數(shù)斤@存。然后設(shè)置線程塊大小和數(shù)量,啟動核函數(shù),最后將結(jié)果影像數(shù)據(jù)從顯存中傳輸?shù)街鞔嬷泻铣山Y(jié)果影像。部分代碼如下所示:

    cudaMalloc((void**)&ImageDevice , ImageSize); //在GPU上分配內(nèi)存空間

    cudaMemcpy(ImagedataDevice,ImagedataHost,ImageSize,cudaMemcpyHostToDevice);//將圖像數(shù)據(jù)由內(nèi)存復(fù)制到顯存中

    dim3 dimBlock(m,n)

    dim3 dimGrid((width+dimBlock.x-1) /dimBlock.x) , (height+dimBlock.y-1) /dimBlock.y) //劃分線程塊大小和數(shù)量

    Kernel<<>>(ImagedataDevice,width,height); //啟動GPU核函數(shù)

    CopyDataFormDevice(ImagedataOut,ImagedataDevice); //將GPU上運算結(jié)果傳輸?shù)街鳈C內(nèi)存

    FreeDeviceAndHost();//釋放主機端和GPU端的內(nèi)存

    3.4 程序優(yōu)化

    經(jīng)過將并行算法映射到GPU中能夠正確運行且結(jié)果驗證準確,才可以在此基礎(chǔ)對程序做進一步的優(yōu)化,來提高程序的性能。平滑算法中每一個像素的計算都使用相同的平滑算子,而且共享存儲器讀寫速度非???,可以被同一線程塊的所有線程訪問。因此為降低對全局存儲器DRAM內(nèi)存的存取,將平滑算子傳入共享存儲器中,從而提高數(shù)據(jù)的存取速度。

    4 實驗結(jié)果與分析

    實驗平臺使用GTX580顯卡,全局存儲器大小為1.5G,共享存儲器為48KB,有16個流多處理器,512個流處理器。CPU為AMD Athlon (tm) II X4 640,內(nèi)存為10G。分別在CPU和單GPU上進行圖像平滑操作。

    測試數(shù)據(jù)為256×256、512×512、1024×1024、2048×2048、4096×4096、8192×8192的灰度圖。將不同分辨率的圖像分別在CPU、原始GPU和程序優(yōu)化后GPU進行平滑處理,對處理時間進行計時,取實驗10次的結(jié)果得到平均執(zhí)行時間。實驗結(jié)果如表1所示。

    表1 算法在不同環(huán)境下的運行時間

    從表1可以看出,在GPU環(huán)境下不同分辨率的圖像進行平滑操作的時間明顯縮短,經(jīng)過程序優(yōu)化之后,執(zhí)行時間又得到了進一步減小。不同分辨率圖像在GPU和優(yōu)化后GPU上運行時間與在CPU上運行時間的加速比曲線如圖4所示。

    圖4 GPU優(yōu)化前后并行算法加速比

    從圖4可以看出隨著圖像分辨率的增大,優(yōu)化前GPU和優(yōu)化后GPU的并行算法加速比曲線都呈上升趨勢,當圖像分辨率為8192×8192時,優(yōu)化前GPU和優(yōu)化后GPU的并行算法加速比都分別達到最大的34.3倍和37.3倍。

    圖5 雙GPU并行處理流程圖

    對圖像平滑算法進行雙GPU試驗時,需要按GPUs圖像并行處理設(shè)計模型的步驟2對任務(wù)進行劃分,將圖像數(shù)據(jù)拆分為兩部分,分別在兩個GPU上并行處理。在雙GPU環(huán)境下,CPU需創(chuàng)建兩個線程分別控制不同的GPU設(shè)備進行圖像處理,然后在CPU中合成最終結(jié)果,處理流程如圖5所示。

    對雙GPU圖像平滑算法進行測試時,使用單GPU實驗圖像數(shù)據(jù),結(jié)果如表2所示。

    表2 單GPU和雙GPU的處理時間比較

    從表2可以看出,當圖像分辨率較低時,雙GPU處理速度稍低于單GPU處理速度,隨著分辨率增加到一定程度,雙GPU處理速度優(yōu)勢才越來越明顯。

    從單GPU和雙GPU兩個實驗結(jié)果中表明,并行設(shè)計后的圖像平滑算法在GPU中取得了很好的加速效果,從而驗證了GPU圖像處理并行設(shè)計模型的有效性。

    5 結(jié)語

    本文在對大量圖像并行算法研究的基礎(chǔ)上,提出了GPU圖像處理并行設(shè)計模型,通過并行平滑算法在GPU中的執(zhí)行從而驗證了模型的有效性。該模型簡單易懂,通用性強,為更多圖像處理算法并行化并移植到GPU中提供了理論基礎(chǔ)。

    [1] 袁濤,馬艷,劉定生.GPU在遙感圖像處理中的應(yīng)用綜述[J].遙感信息,2012,27(6):110-117.

    [2] 方留楊,王密,李德仁.CPU和GPU協(xié)同處理的光學衛(wèi)星遙感影像正射校正方法[J].測繪學報,2013,42(5):668-675.

    [3] 李朋龍,鄧非,何江,等.GPU-CPU協(xié)同航空影像快速正射糾正方法[J].測繪地理信息,2016,41(2):44-47.

    [4] 王化喆,魏先勇.基于GPU的遙感圖像前期處理算法研究與應(yīng)用[J].現(xiàn)代電子技術(shù),2016,39(3):47-50.

    [5] D GRANATA, U AMATO, B ALFANO. MRI denoising by nonlocal means on multi-GPU[J]. Journal of Real-Time Image Processing,2016:1-11.

    [6] 吳頎峰.基于GPU的數(shù)字圖像處理算法研究[D].贛州:江西理工大學,2011.

    [7] 肖漢,張祖勛.基于GPGPU的并行影像匹配算法[J].測繪學報,2010,39(1):46-51.

    [8] 肖漢.基于CPU_GPU的影像匹配高效能異構(gòu)并行計算研究[D].武漢:武漢大學,2011.

    [9] 張舒,褚艷利.GPU高性能運算之CUDA[M].北京:中國水利水電出版社,2009.

    [10] NVIDIA Corporation. CUDA Programming Guide 1.0[EB/OL]. http://www.nvidia.com,2009(8):11.

    [11] 馬安國,成玉,唐遇星,等.GPU異構(gòu)系統(tǒng)中的存儲層次和負載均衡策略研究[J].國防科學技術(shù)大學學報,2009,31(5):38-43.

    Parallel Design Model of GPU Image Processing

    WANG Ping QUAN Jicheng WANG Hongwei

    (Department of Aeronautic and Astromautic Intelligence, Aviation University of Air Force, Changchun 130022)

    The development of GPU general computing provided a new technique for image processing, and some image processing algorithms had been transplanted to GPU and got a better acceleration effect. But it could not form a general parallel design model. Thus, based on the study of the characteristics of GPU structure and the existing parallel algorithms of GPU image processing, this paper proposed a parallel image processing design model of single GPU and multi GPU. And this paper took the algorithm design of parallel image smooth as an example to testify the effectiveness of this model. The experimental results showed that the proposed model had good generality, and it could provide a theoretical reference for the parallel processing of more algorithms in the GPU image processing.

    image algorithms, parallel, GPU, model, generality

    2016年5月6日,

    2016年6月25日

    王平,男,碩士研究生,研究方向:數(shù)字圖像處理和GPU并行計算。全吉成,男,博士,教授,博士生導師,研究方向:二維可視化技術(shù)。王宏偉,男,碩士,講師,研究方向:數(shù)字圖像處理和地理信息系統(tǒng)。

    TN911

    10.3969/j.issn.1672-9730.2016.11.021

    猜你喜歡
    并行算法線程圖像處理
    地圖線要素綜合化的簡遞歸并行算法
    機器學習在圖像處理中的應(yīng)用
    電子制作(2018年18期)2018-11-14 01:48:20
    模糊圖像處理,刑事偵查利器
    圖像處理技術(shù)的實戰(zhàn)應(yīng)用
    淺談linux多線程協(xié)作
    基于GPU的GaBP并行算法研究
    Photo Shop通道在圖像處理中的應(yīng)用
    河南科技(2014年1期)2014-02-27 14:04:06
    基于GPU的分類并行算法的研究與實現(xiàn)
    Linux線程實現(xiàn)技術(shù)研究
    么移動中間件線程池并發(fā)機制優(yōu)化改進
    黑人欧美特级aaaaaa片| 国产av又大| 女人高潮潮喷娇喘18禁视频| 日日夜夜操网爽| 人妻一区二区av| 精品人妻一区二区三区麻豆| 黑人操中国人逼视频| 搡老乐熟女国产| 日韩制服骚丝袜av| 久久狼人影院| 12—13女人毛片做爰片一| 亚洲va日本ⅴa欧美va伊人久久 | 免费一级毛片在线播放高清视频 | 国产av国产精品国产| 制服诱惑二区| 亚洲七黄色美女视频| 黄色视频不卡| 国产视频一区二区在线看| 久久久久国产一级毛片高清牌| 宅男免费午夜| 国产精品一二三区在线看| 欧美国产精品一级二级三级| 亚洲av电影在线进入| 亚洲国产精品999| 久久国产精品男人的天堂亚洲| 亚洲 国产 在线| 真人做人爱边吃奶动态| 免费在线观看黄色视频的| 国产又爽黄色视频| 日韩中文字幕欧美一区二区| 最新在线观看一区二区三区| 三级毛片av免费| 男女下面插进去视频免费观看| 久久狼人影院| 亚洲伊人色综图| 在线亚洲精品国产二区图片欧美| 老司机在亚洲福利影院| 免费一级毛片在线播放高清视频 | 一边摸一边做爽爽视频免费| 欧美激情久久久久久爽电影 | 19禁男女啪啪无遮挡网站| 午夜激情久久久久久久| 少妇粗大呻吟视频| 日韩欧美免费精品| 91大片在线观看| 飞空精品影院首页| 国内毛片毛片毛片毛片毛片| 在线av久久热| 丝袜脚勾引网站| 国产一区有黄有色的免费视频| 久久性视频一级片| 国产一区二区 视频在线| 女人高潮潮喷娇喘18禁视频| 亚洲精品久久久久久婷婷小说| 欧美少妇被猛烈插入视频| 精品福利永久在线观看| 亚洲欧洲日产国产| 午夜精品国产一区二区电影| 精品视频人人做人人爽| 嫁个100分男人电影在线观看| netflix在线观看网站| 男人添女人高潮全过程视频| 亚洲av日韩精品久久久久久密| 午夜福利影视在线免费观看| 欧美日本中文国产一区发布| 在线亚洲精品国产二区图片欧美| 交换朋友夫妻互换小说| 高清在线国产一区| 老司机亚洲免费影院| 在线观看免费视频网站a站| 国产黄色免费在线视频| 窝窝影院91人妻| 日韩欧美一区二区三区在线观看 | 青青草视频在线视频观看| 亚洲国产成人一精品久久久| 欧美精品一区二区大全| 国产成人免费无遮挡视频| 久久久精品免费免费高清| 99精品久久久久人妻精品| 亚洲精品第二区| 亚洲精品中文字幕一二三四区 | 涩涩av久久男人的天堂| 中文字幕人妻丝袜制服| 亚洲九九香蕉| 天堂8中文在线网| 精品国产一区二区三区久久久樱花| 777米奇影视久久| 十八禁高潮呻吟视频| 亚洲av欧美aⅴ国产| 99热全是精品| 成人手机av| 婷婷成人精品国产| 女警被强在线播放| 国产精品免费视频内射| 一个人免费在线观看的高清视频 | 国产精品免费视频内射| 熟女少妇亚洲综合色aaa.| 中文字幕最新亚洲高清| 久久 成人 亚洲| 男女国产视频网站| 最黄视频免费看| 日本a在线网址| 亚洲男人天堂网一区| 老汉色av国产亚洲站长工具| 少妇 在线观看| 日本一区二区免费在线视频| 亚洲专区国产一区二区| 一级,二级,三级黄色视频| 热99国产精品久久久久久7| 亚洲av电影在线进入| 免费一级毛片在线播放高清视频 | 亚洲精品美女久久久久99蜜臀| 在线亚洲精品国产二区图片欧美| 国产在视频线精品| 日韩大片免费观看网站| 成在线人永久免费视频| 天堂俺去俺来也www色官网| 丰满迷人的少妇在线观看| 久久ye,这里只有精品| 国产三级黄色录像| 窝窝影院91人妻| 国产精品一区二区在线观看99| xxxhd国产人妻xxx| 亚洲中文av在线| 又黄又粗又硬又大视频| 国产不卡av网站在线观看| 亚洲av电影在线观看一区二区三区| 国产不卡av网站在线观看| 国产一区二区 视频在线| 国产xxxxx性猛交| 18禁黄网站禁片午夜丰满| 国产精品免费视频内射| 超色免费av| 麻豆乱淫一区二区| 波多野结衣一区麻豆| 欧美久久黑人一区二区| 亚洲欧美日韩另类电影网站| 视频在线观看一区二区三区| 999久久久精品免费观看国产| 亚洲熟女精品中文字幕| 激情视频va一区二区三区| 久久精品国产亚洲av高清一级| 欧美中文综合在线视频| 亚洲视频免费观看视频| 中文字幕av电影在线播放| www.av在线官网国产| 丰满少妇做爰视频| 大香蕉久久网| 亚洲一卡2卡3卡4卡5卡精品中文| 美国免费a级毛片| 国产成人系列免费观看| 国产成人精品无人区| 一级a爱视频在线免费观看| 嫁个100分男人电影在线观看| 丝袜在线中文字幕| 性少妇av在线| 在线观看一区二区三区激情| 亚洲av日韩在线播放| 亚洲专区国产一区二区| 99精品久久久久人妻精品| 精品亚洲成a人片在线观看| 国产一区二区三区av在线| 婷婷成人精品国产| 日本vs欧美在线观看视频| 丰满饥渴人妻一区二区三| 国产欧美日韩一区二区精品| 悠悠久久av| 亚洲成国产人片在线观看| 在线观看一区二区三区激情| 老熟女久久久| 下体分泌物呈黄色| 欧美日韩福利视频一区二区| 国产一区有黄有色的免费视频| 亚洲欧美一区二区三区黑人| 亚洲精品成人av观看孕妇| 久久香蕉激情| 欧美黄色淫秽网站| 久久精品aⅴ一区二区三区四区| 中文字幕av电影在线播放| 精品人妻一区二区三区麻豆| 爱豆传媒免费全集在线观看| 另类亚洲欧美激情| 亚洲精品av麻豆狂野| 人人妻人人澡人人爽人人夜夜| 亚洲中文日韩欧美视频| 亚洲国产精品一区二区三区在线| 日韩免费高清中文字幕av| a在线观看视频网站| 亚洲 欧美一区二区三区| 99精国产麻豆久久婷婷| 一级黄色大片毛片| 亚洲av电影在线进入| 少妇 在线观看| 国产精品秋霞免费鲁丝片| 青春草视频在线免费观看| 精品少妇久久久久久888优播| 啦啦啦 在线观看视频| 我要看黄色一级片免费的| 伊人亚洲综合成人网| 午夜精品国产一区二区电影| 老汉色∧v一级毛片| 777久久人妻少妇嫩草av网站| 亚洲成国产人片在线观看| 精品免费久久久久久久清纯 | 亚洲精品自拍成人| 亚洲精品国产av成人精品| 中文字幕另类日韩欧美亚洲嫩草| 999久久久精品免费观看国产| 成年人免费黄色播放视频| 大香蕉久久成人网| 亚洲中文日韩欧美视频| 国产成人精品无人区| 999久久久国产精品视频| 天堂8中文在线网| 中文精品一卡2卡3卡4更新| 国产一区二区激情短视频 | 少妇被粗大的猛进出69影院| 好男人电影高清在线观看| 国产深夜福利视频在线观看| 精品一品国产午夜福利视频| 中国国产av一级| 一级,二级,三级黄色视频| 亚洲第一av免费看| 日日摸夜夜添夜夜添小说| 色94色欧美一区二区| 日韩中文字幕欧美一区二区| 午夜精品久久久久久毛片777| 超碰97精品在线观看| 国产精品免费大片| 国产亚洲精品久久久久5区| 久久久久久久大尺度免费视频| 丰满人妻熟妇乱又伦精品不卡| 肉色欧美久久久久久久蜜桃| 999久久久国产精品视频| 91大片在线观看| 最新的欧美精品一区二区| 日韩欧美一区视频在线观看| av电影中文网址| 午夜老司机福利片| 国产欧美日韩精品亚洲av| 精品福利观看| 日本vs欧美在线观看视频| 亚洲精品美女久久久久99蜜臀| 国产精品久久久久成人av| 可以免费在线观看a视频的电影网站| 欧美激情极品国产一区二区三区| 丰满饥渴人妻一区二区三| 精品一区在线观看国产| 亚洲精品美女久久久久99蜜臀| 高清欧美精品videossex| 欧美日韩一级在线毛片| 不卡一级毛片| 91老司机精品| 男人操女人黄网站| 在线精品无人区一区二区三| 啦啦啦啦在线视频资源| 青春草亚洲视频在线观看| 亚洲一码二码三码区别大吗| 午夜福利视频在线观看免费| 真人做人爱边吃奶动态| 人人妻人人澡人人看| 久久精品熟女亚洲av麻豆精品| 中文字幕精品免费在线观看视频| 日韩一卡2卡3卡4卡2021年| 日韩三级视频一区二区三区| 久久人人爽人人片av| 国产三级黄色录像| 伊人久久大香线蕉亚洲五| 中国国产av一级| 久久精品亚洲av国产电影网| 另类亚洲欧美激情| 国产在视频线精品| 母亲3免费完整高清在线观看| 欧美精品亚洲一区二区| 夫妻午夜视频| 男女无遮挡免费网站观看| 不卡av一区二区三区| 男人操女人黄网站| 十八禁网站网址无遮挡| 啦啦啦中文免费视频观看日本| 人人妻,人人澡人人爽秒播| 亚洲国产欧美在线一区| 国产精品久久久av美女十八| 无限看片的www在线观看| 一本—道久久a久久精品蜜桃钙片| 国产一区二区三区在线臀色熟女 | 超色免费av| 午夜免费成人在线视频| 自拍欧美九色日韩亚洲蝌蚪91| 国产伦理片在线播放av一区| 国产免费福利视频在线观看| 婷婷色av中文字幕| 亚洲精品第二区| 正在播放国产对白刺激| 一本大道久久a久久精品| 国产精品亚洲av一区麻豆| 美女高潮到喷水免费观看| 国产日韩欧美视频二区| 国产欧美日韩综合在线一区二区| 90打野战视频偷拍视频| 久久女婷五月综合色啪小说| 国产亚洲精品久久久久5区| 亚洲久久久国产精品| 日韩免费高清中文字幕av| 99久久99久久久精品蜜桃| 青春草亚洲视频在线观看| 我的亚洲天堂| 日韩制服骚丝袜av| 中国美女看黄片| 国产xxxxx性猛交| 一边摸一边做爽爽视频免费| 久久 成人 亚洲| 青青草视频在线视频观看| 夫妻午夜视频| 操美女的视频在线观看| 国产一区二区三区av在线| a级毛片在线看网站| 国产精品av久久久久免费| 成人黄色视频免费在线看| 久久精品亚洲av国产电影网| 亚洲第一欧美日韩一区二区三区 | 欧美午夜高清在线| 黄片小视频在线播放| 久久中文字幕一级| 黄片大片在线免费观看| 欧美精品一区二区免费开放| 国产一区二区三区av在线| 国产精品99久久99久久久不卡| 成人18禁高潮啪啪吃奶动态图| 国产精品亚洲av一区麻豆| 波多野结衣一区麻豆| 日本精品一区二区三区蜜桃| 女人被躁到高潮嗷嗷叫费观| 在线十欧美十亚洲十日本专区| 午夜日韩欧美国产| 日本av手机在线免费观看| 男女高潮啪啪啪动态图| 欧美日韩亚洲国产一区二区在线观看 | 欧美人与性动交α欧美精品济南到| 老鸭窝网址在线观看| 肉色欧美久久久久久久蜜桃| 久久久国产精品麻豆| 精品人妻熟女毛片av久久网站| 热99久久久久精品小说推荐| 成年动漫av网址| 美女中出高潮动态图| 国产又爽黄色视频| 午夜影院在线不卡| 欧美av亚洲av综合av国产av| 亚洲av成人不卡在线观看播放网 | 日韩熟女老妇一区二区性免费视频| 十八禁网站网址无遮挡| 亚洲av美国av| 一本一本久久a久久精品综合妖精| 国产欧美日韩一区二区三 | 久久亚洲精品不卡| 一区福利在线观看| 午夜免费观看性视频| 午夜福利乱码中文字幕| 亚洲精品久久成人aⅴ小说| av欧美777| 80岁老熟妇乱子伦牲交| 80岁老熟妇乱子伦牲交| av视频免费观看在线观看| 国产主播在线观看一区二区| 亚洲精品久久成人aⅴ小说| 欧美黑人精品巨大| 国产免费av片在线观看野外av| 国产免费av片在线观看野外av| 国产免费av片在线观看野外av| 日韩欧美一区二区三区在线观看 | 蜜桃国产av成人99| 中文字幕制服av| 丝瓜视频免费看黄片| 涩涩av久久男人的天堂| 亚洲欧美色中文字幕在线| 亚洲第一av免费看| 欧美黑人精品巨大| 亚洲成人国产一区在线观看| 精品人妻熟女毛片av久久网站| 亚洲精品中文字幕一二三四区 | 女人被躁到高潮嗷嗷叫费观| 狠狠精品人妻久久久久久综合| 老熟女久久久| 国产一区有黄有色的免费视频| 国产又爽黄色视频| 国产免费av片在线观看野外av| 宅男免费午夜| 精品人妻熟女毛片av久久网站| 亚洲精品一二三| 老汉色av国产亚洲站长工具| 久久精品人人爽人人爽视色| 国产成人精品在线电影| 视频区欧美日本亚洲| 肉色欧美久久久久久久蜜桃| 亚洲黑人精品在线| 91国产中文字幕| 一区在线观看完整版| 精品国产一区二区久久| 精品久久蜜臀av无| 黑人猛操日本美女一级片| 两个人看的免费小视频| 少妇猛男粗大的猛烈进出视频| 夜夜骑夜夜射夜夜干| 日韩欧美国产一区二区入口| 永久免费av网站大全| 亚洲 欧美一区二区三区| 美女中出高潮动态图| 麻豆av在线久日| 国产激情久久老熟女| a级毛片黄视频| 亚洲国产看品久久| cao死你这个sao货| 免费久久久久久久精品成人欧美视频| 妹子高潮喷水视频| 男人添女人高潮全过程视频| 午夜免费成人在线视频| 欧美变态另类bdsm刘玥| 日韩三级视频一区二区三区| 亚洲国产精品一区二区三区在线| 久久免费观看电影| 亚洲欧美成人综合另类久久久| 熟女少妇亚洲综合色aaa.| 中国国产av一级| 女人爽到高潮嗷嗷叫在线视频| 亚洲专区国产一区二区| 国产精品久久久久成人av| 日韩中文字幕欧美一区二区| 国产日韩欧美亚洲二区| 久久中文看片网| 久久中文字幕一级| 欧美大码av| 亚洲 国产 在线| 久久中文字幕一级| 2018国产大陆天天弄谢| 一级a爱视频在线免费观看| 久久天堂一区二区三区四区| 桃红色精品国产亚洲av| 91字幕亚洲| 一级黄色大片毛片| 极品少妇高潮喷水抽搐| 在线永久观看黄色视频| 黑丝袜美女国产一区| 汤姆久久久久久久影院中文字幕| 热99re8久久精品国产| 国产精品欧美亚洲77777| 少妇猛男粗大的猛烈进出视频| 国产精品久久久久久精品电影小说| 每晚都被弄得嗷嗷叫到高潮| 国产精品香港三级国产av潘金莲| av有码第一页| 汤姆久久久久久久影院中文字幕| 一本—道久久a久久精品蜜桃钙片| 天堂8中文在线网| a级毛片黄视频| 精品人妻1区二区| 99re6热这里在线精品视频| 欧美在线一区亚洲| 亚洲av男天堂| 国产精品久久久久久精品电影小说| videosex国产| 日本av手机在线免费观看| 国产av一区二区精品久久| 亚洲国产av新网站| 欧美日韩亚洲高清精品| 欧美成狂野欧美在线观看| 国产精品欧美亚洲77777| 女人爽到高潮嗷嗷叫在线视频| 亚洲精品中文字幕在线视频| 一区二区日韩欧美中文字幕| 日韩视频一区二区在线观看| 午夜福利在线观看吧| 18禁裸乳无遮挡动漫免费视频| 中国美女看黄片| 国产区一区二久久| 久久青草综合色| 久久久久国产精品人妻一区二区| 午夜两性在线视频| 在线观看免费视频网站a站| 久久人妻福利社区极品人妻图片| 最黄视频免费看| 久久久久久久久免费视频了| 九色亚洲精品在线播放| 波多野结衣av一区二区av| 啦啦啦 在线观看视频| 男女之事视频高清在线观看| 天天操日日干夜夜撸| 亚洲成国产人片在线观看| 丝袜美足系列| 超碰97精品在线观看| 国产精品麻豆人妻色哟哟久久| 国产免费av片在线观看野外av| 国产成人精品无人区| 成人国语在线视频| 天天躁日日躁夜夜躁夜夜| 嫩草影视91久久| 女性生殖器流出的白浆| 波多野结衣一区麻豆| 91大片在线观看| 国产精品久久久av美女十八| 操美女的视频在线观看| 成年av动漫网址| 国产av又大| 高潮久久久久久久久久久不卡| 黄网站色视频无遮挡免费观看| 国产精品久久久人人做人人爽| 一级片免费观看大全| 夫妻午夜视频| 一二三四在线观看免费中文在| 日韩电影二区| 国产成人精品久久二区二区91| 91麻豆av在线| 美女国产高潮福利片在线看| 日韩精品免费视频一区二区三区| 国产成人精品无人区| 黑人欧美特级aaaaaa片| 日韩一区二区三区影片| 精品乱码久久久久久99久播| 国产精品偷伦视频观看了| 两个人看的免费小视频| 超碰97精品在线观看| 捣出白浆h1v1| 亚洲av日韩精品久久久久久密| 国产欧美日韩一区二区精品| 国产99久久九九免费精品| 中文字幕制服av| 色94色欧美一区二区| 99热网站在线观看| 亚洲自偷自拍图片 自拍| 欧美97在线视频| 色精品久久人妻99蜜桃| 丰满迷人的少妇在线观看| 亚洲成人免费电影在线观看| 欧美激情 高清一区二区三区| 91成年电影在线观看| 亚洲色图 男人天堂 中文字幕| 老司机福利观看| 黑人操中国人逼视频| 亚洲国产毛片av蜜桃av| 啪啪无遮挡十八禁网站| 国产精品一区二区在线不卡| 999精品在线视频| 午夜福利免费观看在线| 久久久久视频综合| 国产精品免费视频内射| 91精品三级在线观看| 亚洲国产av新网站| 五月天丁香电影| 久久中文看片网| 国产成人av教育| 免费在线观看视频国产中文字幕亚洲 | 黄色视频在线播放观看不卡| 亚洲第一青青草原| 一进一出抽搐动态| 热99国产精品久久久久久7| 精品人妻在线不人妻| av视频免费观看在线观看| 欧美人与性动交α欧美精品济南到| 99九九在线精品视频| 久热这里只有精品99| 欧美日韩福利视频一区二区| 一本大道久久a久久精品| 亚洲一区中文字幕在线| 午夜福利,免费看| 欧美激情高清一区二区三区| 久久久久精品国产欧美久久久 | av在线播放精品| 亚洲欧美色中文字幕在线| 桃红色精品国产亚洲av| 亚洲精品一卡2卡三卡4卡5卡 | 男人爽女人下面视频在线观看| 午夜福利,免费看| 丰满人妻熟妇乱又伦精品不卡| 成人av一区二区三区在线看 | 国产精品欧美亚洲77777| 久久久久国产精品人妻一区二区| 国产亚洲欧美在线一区二区| 日韩大片免费观看网站| 一边摸一边做爽爽视频免费| 亚洲,欧美精品.| 超色免费av| 又黄又粗又硬又大视频| 肉色欧美久久久久久久蜜桃| 在线av久久热| 欧美日韩精品网址| 精品久久久久久久毛片微露脸 | 国产不卡av网站在线观看| 黄片大片在线免费观看| 久久ye,这里只有精品| 日韩制服丝袜自拍偷拍| 成年人黄色毛片网站| 国产精品久久久久久精品古装| 国产成人精品久久二区二区91| 一本大道久久a久久精品| 中文字幕人妻丝袜一区二区| 国产高清国产精品国产三级| 人人妻,人人澡人人爽秒播| 91国产中文字幕| 又黄又粗又硬又大视频| 久久狼人影院| av网站在线播放免费| 啦啦啦啦在线视频资源| 丝袜美腿诱惑在线| 欧美少妇被猛烈插入视频| 在线观看www视频免费| 男女下面插进去视频免费观看| 国产激情久久老熟女| 在线亚洲精品国产二区图片欧美| 大陆偷拍与自拍| 国产亚洲欧美精品永久| 亚洲 国产 在线| 精品福利永久在线观看| 中文字幕色久视频| 久久国产精品影院| 女人久久www免费人成看片|