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

    基于GPU加速的快速字符串匹配算法

    2015-04-02 12:08:40續(xù)士強(qiáng)祝永志
    軟件導(dǎo)刊 2015年2期
    關(guān)鍵詞:并行計(jì)算

    續(xù)士強(qiáng) 祝永志

    摘要:如何提高字符串實(shí)際匹配效率一直是信息匹配領(lǐng)域中非常重要的研究課題。在分析字符串匹配并行規(guī)律的基礎(chǔ)上,結(jié)合GPU并行體系結(jié)構(gòu),對(duì)Sunday算法實(shí)現(xiàn)并行化。在CPU和GPU不同計(jì)算平臺(tái)上分別做了對(duì)比實(shí)驗(yàn),實(shí)驗(yàn)結(jié)果顯示基于GPU并行實(shí)現(xiàn)的Sunday算法比傳統(tǒng)Sunday算法具有更高的匹配速度。

    關(guān)鍵詞關(guān)鍵詞:CUDA;Sunday算法;并行計(jì)算

    DOIDOI:10.11907/rjdk.143766

    中圖分類號(hào):TP312

    文獻(xiàn)標(biāo)識(shí)碼:A文章編號(hào)文章編號(hào):16727800(2015)002005103

    基金項(xiàng)目基金項(xiàng)目:山東省自然科學(xué)基金項(xiàng)目(ZR2013FL015);山東省研究生教育創(chuàng)新資助計(jì)劃項(xiàng)目(SDYY12060)

    作者簡介作者簡介:續(xù)士強(qiáng)(1990-),男,山東滕州人,曲阜師范大學(xué)信息科學(xué)與工程學(xué)院碩士研究生,研究方向?yàn)榫W(wǎng)絡(luò)與并行計(jì)算;祝永志(1964-),男,吉林榆樹人,曲阜師范大學(xué)信息科學(xué)與工程學(xué)院教授、碩士生導(dǎo)師,研究方向?yàn)榫W(wǎng)絡(luò)與并行計(jì)算。

    0引言

    字符串匹配被廣泛應(yīng)用于解決搜索引擎、網(wǎng)絡(luò)入侵檢測、計(jì)算機(jī)病毒特征碼匹配以及DNA序列匹配等諸多問題中。目前關(guān)于字符串匹配算法的研究已經(jīng)相對(duì)成熟,傳統(tǒng)的串匹配算法實(shí)現(xiàn)思想主要分為前綴搜索、后綴搜索和子串搜索,經(jīng)典的算法[1]有KMP算法、Shift-And算法、BM算法、BDM算法等等。然而傳統(tǒng)算法在實(shí)際應(yīng)用中并沒有表現(xiàn)理論上的優(yōu)勢,比如,在一個(gè)普通文本文件中查找字符串,BF算法用的時(shí)間通常比KMP算法要少,即使后者在時(shí)間復(fù)雜度上要優(yōu)于前者。因此,選擇一種在實(shí)際應(yīng)用中性能較好的算法,對(duì)于提高效率至關(guān)重要。

    隨著圖形處理器性能的不斷提高,特別是通用并行計(jì)算架構(gòu)(CUDA)的推出,圖形處理器已不再局限于圖形圖像處理,其在通用計(jì)算方面已經(jīng)遠(yuǎn)遠(yuǎn)超越了CPU。由于GPU的特點(diǎn)就是處理密集型數(shù)據(jù)和并行數(shù)據(jù)計(jì)算,因此,CUDA編程模型非常適合解決大規(guī)模并行計(jì)算問題。

    1CUDA編程模型

    CUDA(Compute Unified Device Architecture),是由NVIDIA推出的通用并行計(jì)算架構(gòu),它在C語言基礎(chǔ)上添加了適用于GPU并行計(jì)算的API和開發(fā)庫,是在GPU強(qiáng)大計(jì)算能力基礎(chǔ)上建立的效率更高的密集數(shù)據(jù)計(jì)算解決方案。

    在NVIDIA的GPU中,最基本的處理單元是SP(流處理器),多個(gè)SP組成一個(gè)SM(流多處理器),它們之間可以共享控制邏輯和指令緩存。在CUDA編程下,程序執(zhí)行的最小單位是thread(線程),每個(gè)thread都有各自的一份register和local memory。一組thread組成一個(gè)block(線程塊),在同一個(gè)block中的thread可以存取同一塊共享內(nèi)存,最后執(zhí)行同一kernel函數(shù)的block構(gòu)成一個(gè)grid(塊網(wǎng)格)。CUDA架構(gòu)下的程序包括運(yùn)行在CPU上負(fù)責(zé)串行執(zhí)行的Host端,以及運(yùn)行在GPU上作并行計(jì)算的Device端。Kernel函數(shù)由host端調(diào)用,能生成大量的線程,每個(gè)線程處理對(duì)應(yīng)的數(shù)據(jù)塊,從而實(shí)現(xiàn)了數(shù)據(jù)的并行處理。grid的所有線程都執(zhí)行同一個(gè)kernel函數(shù)。CUDA的device在實(shí)際執(zhí)行時(shí),以block為單位,并將每個(gè)block分給SM執(zhí)行,同一block中的thread,又以32個(gè)組成一個(gè)warp一起執(zhí)行。每個(gè)SM只執(zhí)行一個(gè)block中的warp,由于在實(shí)際執(zhí)行過程中,某個(gè)warp需要訪問全局存儲(chǔ)器,這時(shí)SM就會(huì)切換到別的warp來繼續(xù)執(zhí)行。因此,一個(gè)SM可以同時(shí)處理多個(gè)block。

    2基于GPU的Sunday算法并行化

    2.1Sunday字符串匹配算法

    Sunday算法源于BM算法充分利用壞字符的思想。Sunday算法將計(jì)算好后綴的時(shí)間節(jié)約下來,將所有情況歸為壞字符規(guī)則來匹配,這對(duì)短模式串匹配十分有利。因此,Sunday算法的匹配過程基本應(yīng)用的就是BM算法的壞字符規(guī)則,即當(dāng)字符串不匹配時(shí),判斷目標(biāo)串進(jìn)行匹配的下一字符是否在模式串中出現(xiàn),如果出現(xiàn),則模式串移動(dòng)到目標(biāo)串中最右端的該字符串的下一位置;如果沒有出現(xiàn),則模式串直接跳過模式串字符長度。

    Sunday算法實(shí)現(xiàn)如下:

    while(main_i

    {

    int tem=main_i;

    while(sub_j

    {

    if(mainStr[main_i] == subStr[sub_j])

    {

    main_i++;

    sub_j++;

    continue;

    }

    else{

    if(tem+subStrLen > mainStrLen)

    return -1;

    char firstRightChar=

    mainStr[tem+subStrLen];

    main_i+=

    char step[(unsigned char)firstRightChar];

    sub_j=0;

    break;

    }

    }

    if(sub_j == subStrLen)

    return main_i-subStrLen;

    }

    2.2字符串并行劃分設(shè)計(jì)

    CUDA編程模型是基于并行執(zhí)行多個(gè)線程來實(shí)現(xiàn)大規(guī)??焖儆?jì)算的,因此字符串要實(shí)現(xiàn)并行匹配,就必須將原有的字符串劃分成多個(gè)小字符串,再將小字符串分散到各個(gè)線程中,線程對(duì)分配的小字符串進(jìn)行匹配。但是,僅僅做到簡單劃分是不夠的,通常串行的字符串匹配算法,無論算法如何設(shè)計(jì)向前跳躍,匹配始終帶有一定的順序性,在劃分后的局部字符串匹配位置必須到下一小字符串才能找到。為了解決劃分字符串過程中存在的漏解問題,采用冗余數(shù)據(jù)是簡單可行的方法。

    假設(shè)將長度為T的文本串均勻分成互不重疊的m段,分布在0~(m-1)線程中,則顯然每個(gè)線程中字符串長度為[n/m],再將長度為s的模式串分配到各個(gè)線程,使得每個(gè)線程都對(duì)分到的小字符串進(jìn)行匹配[3]。為了解決漏解問題,在每個(gè)線程分得的小字符串末尾位置存儲(chǔ)與其相鄰的長度為s-1的字符串。

    2.3Sunday算法并行實(shí)現(xiàn)

    串行實(shí)現(xiàn)的Sunday算法,通過極少的比較次數(shù)來獲得較大的跳躍距離,與BF算法相比,避免了大量回溯匹配的產(chǎn)生。而基于GPU這種并行體系結(jié)構(gòu)的并行算法,利用多個(gè)線程并行執(zhí)行解決問題,原有較長的字符串劃分到各個(gè)線程,使得每個(gè)線程字符串長度明顯縮短,比串行集中式的匹配算法速度提高很多。

    2.3.1數(shù)據(jù)預(yù)處理

    為了最大限度地利用CPU資源,目標(biāo)串的存取與分片工作放在CPU進(jìn)行。首先在內(nèi)存中分配一塊大致與目標(biāo)串物理存儲(chǔ)大小相等的存取空間。比如目標(biāo)串存儲(chǔ)的文本大小為10M,那么就在內(nèi)存中申請(qǐng)大約10M的地址空間,目的是為了使目標(biāo)串讀入主存,便于程序存取。當(dāng)然,實(shí)際申請(qǐng)地址空間時(shí),空間大小是根據(jù)讀取到的目標(biāo)串大小而設(shè)定的。通過I/O操作將目標(biāo)串從外部文件讀入到內(nèi)存后,對(duì)目標(biāo)串進(jìn)行如下分片操作:

    (1)根據(jù)目標(biāo)串的總長度與CUDA的線程數(shù)來確定每個(gè)線程要處理字符串的長度。雖然GPU可以創(chuàng)建上百萬甚至上千萬線程,但是同時(shí)并行的線程總數(shù)卻十分有限。因此,創(chuàng)建合理數(shù)量的線程不僅可以避免一些額外開銷,而且可以提升算法總體效率。以GT750M為例,每個(gè)block最多可以同時(shí)運(yùn)行的線程數(shù)是2 048,但根據(jù)實(shí)驗(yàn)結(jié)果,取1 024比較好。這是因?yàn)槊總€(gè)CUDA線程處理性能有限,分片后小字符串如果太長,線程匹配耗時(shí)增加,算法的整體匹配效率會(huì)變差。如果太短,那么分配的線程總數(shù)就多,用于線程分配和回收的額外時(shí)間大大增加,算法的效率就得不到提高。因此,合理的分片對(duì)于最終匹配效果十分重要。經(jīng)過實(shí)驗(yàn),分片后的小字符串長度驗(yàn)證取64為宜。

    (2)字符串的漏解處理[4]。由于對(duì)字符串進(jìn)行了分片操作,小字符串末尾和開始位置的字符就喪失了原來的順序,同一串的字符分到不同線程,而這一字符串可能恰好是匹配串,這樣就造成匹配過程的漏解情況。為了解決這個(gè)問題,必須在每個(gè)小字符串后面添加下一段字符串的前m-1個(gè)的字符(m為模式串長度)。這里需要說明的是,添加冗余數(shù)據(jù)的處理在CPU端進(jìn)行。由于模式串的長度相對(duì)較短,即使在分片較多的情況下,所添加的冗余字符對(duì)算法的匹配效率也不會(huì)造成大的影響。需要注意的是,添加冗余字符后,模式串的實(shí)際匹配位置需要作移位處理,保持結(jié)果正確。

    2.3.2并行匹配

    改進(jìn)算法對(duì)字符串實(shí)際匹配操作都是在GPU中完成的,因此目標(biāo)串要再從內(nèi)存讀取到顯存,與內(nèi)存申請(qǐng)地址空間類似。通過cudaMalloc函數(shù)在顯存中申請(qǐng)地址空間,然后再調(diào)用cudaMemcpy函數(shù)將內(nèi)存中的目標(biāo)串復(fù)制到顯存中。這樣,GPU就能直接對(duì)顯存中的目標(biāo)串進(jìn)行匹配操作。調(diào)用kernel函數(shù)完成字符的匹配后,再把顯存存儲(chǔ)的匹配結(jié)果復(fù)制到內(nèi)存的變量中進(jìn)行顯示。

    Kernel函數(shù)對(duì)字符串匹配操作過程:①根據(jù)blockIdx與threadIdx變量確定當(dāng)前線程的實(shí)際線程號(hào);②根據(jù)線程號(hào)找到要處理的字符串位置;③對(duì)每個(gè)小字符串實(shí)現(xiàn)Sunday算法。每個(gè)線程處理字符串長度與分片后的小字符串長度一致。

    Kernel函數(shù)的部分代碼如下:

    __global__ void sunday_kernel(char *g_subStr,int subStr_len,int aim_len,char *aim_text,int *gpu_pos)

    {

    int i=threadIdx.x+threadIdx.y*16+blockIdx.x*256;

    int j=0;

    int c = 0; //計(jì)數(shù)

    int m = i*64;

    int n = 0;

    while(m+n

    if(aim_text[m+n]== g_subStr [j])

    {

    n++;

    j++;

    count++;

    }

    else {

    n++;

    j = 0;

    count = 0;

    }

    if(c== subStr_len)

    {

    *gpu_pos = m+n-count;

    }

    }

    3實(shí)驗(yàn)結(jié)果與分析

    實(shí)驗(yàn)環(huán)境硬件配置:CPU:Intel Core i5-3230M,主頻:2.60GHz,內(nèi)存:4GB。GPU采用GT750M 核心頻率950MHz,顯存2G。操作系統(tǒng)是Windows XP professional 2002 Service Package 3,軟件平臺(tái)為CUDA 5.5,實(shí)驗(yàn)集成環(huán)境Visual Studio 2010。

    使用人類基因DNA部分序列集合字符串作為文本串匹配數(shù)據(jù)集。本文第一組實(shí)驗(yàn),測試在相同文本大小的目標(biāo)串情況下,不同匹配算法消耗的匹配時(shí)間對(duì)比,實(shí)驗(yàn)文本大小為30M,模式串為“test”,實(shí)驗(yàn)結(jié)果見表1,匹配時(shí)間結(jié)果以ms為單位;第二組實(shí)驗(yàn),測試CPU與GPU固定模式串長度在不同文本大小字符串的匹配時(shí)間對(duì)比,實(shí)驗(yàn)過程中對(duì)字符串文本隨機(jī)插入模式串“test”,再對(duì)模式串進(jìn)行匹配,實(shí)驗(yàn)結(jié)果見表2,匹配時(shí)間以ms為單位,匹配位置單位為字符個(gè)數(shù)。

    表1不同算法消耗的匹配時(shí)間對(duì)比

    []BF算法[]KMP算法[]Sunday算法

    匹配時(shí)間(ms)[]85.784 66[]215.690 48[]73.988 68

    匹配位置[]32 157 335[]32 157 335[]32 157 335

    表2Sunday算法與GPU并行Sunday算法字符串匹配消耗時(shí)間對(duì)比

    文本大小[]1M[]8M[]16M[]30M[]53M[]77M

    CPU匹配時(shí)間(ms)[]2.942 78[]20.341 69[]40.153 63[]75.152 00[]133.682 68[]191.519 03

    GPU匹配時(shí)間(ms)[]2.008 25[]7.455 17[]14.277 82[]25.333 25[]43.330 85[]61.758 17

    匹配匹配位置[]1 024 997[]8 353 018[]17 037 000[]32 157 327[]55 622 541[]80 752 081

    從第一組實(shí)驗(yàn)結(jié)果可以看出,在相同文本大小的目標(biāo)串和相同的模式串情況下,Sunday算法的匹配時(shí)間最短,BF算法次之,而KMP算法匹配時(shí)間最長。傳統(tǒng)的字符串匹配算法實(shí)現(xiàn)的基本思路是,根據(jù)模式串按照從左到右或從右到左的順序依次與模式串匹配,若不匹配,則根據(jù)相應(yīng)規(guī)則進(jìn)行移位跳躍。大部分的字符串匹配算法只是對(duì)如何進(jìn)行移位跳躍進(jìn)行改進(jìn),而這個(gè)改進(jìn)還必須根據(jù)模式串的自身結(jié)構(gòu)是否具有前后綴匹配來實(shí)現(xiàn)。實(shí)際應(yīng)用中,特別是文本字符串匹配時(shí),輸入的模式串很難經(jīng)常有前后綴自相匹配的情況。因此,針對(duì)于這方面的改進(jìn)算法,匹配時(shí)間比BF算法沒有明顯的降低,甚至比BF算法耗費(fèi)的時(shí)間更長,這是因?yàn)楦倪M(jìn)算法在移動(dòng)跳躍之前,還要對(duì)模式串遍歷和比較。而Sunday算法通過模式串尾部字符與目標(biāo)串相應(yīng)字符比較,獲得盡可能大的跳躍距離,避免了重復(fù)字符匹配。因此,Sunday算法大大提高了匹配效率。

    由表2實(shí)驗(yàn)結(jié)果可以看出,在不同大小的文本字符串匹配中,GPU并行的Sunday算法與傳統(tǒng)Sunday算法維持約3倍的加速比。GPU先天強(qiáng)大的并行處理能力為字符串并行匹配提供了良好的工具。在實(shí)際程序運(yùn)行中,GPU線程的分配和結(jié)果數(shù)據(jù)的回傳占用了較多的時(shí)間,盡管如此,字符串的匹配速度還是獲得了較大的提升。與此同時(shí),將模式串存儲(chǔ)到共享內(nèi)存的方式也避免了頻繁訪問顯存帶來的額外時(shí)間開銷,因?yàn)轱@存的讀寫速度比共享內(nèi)存的速度慢得多。

    4結(jié)語

    本文在分析字符串匹配并行執(zhí)行特點(diǎn)的基礎(chǔ)上,利用GPU數(shù)據(jù)并行化的架構(gòu)特點(diǎn),設(shè)計(jì)出適合于GPU運(yùn)行的快速字符串匹配算法。雖然算法使得字符串匹配速度有所提升,但是還有較大的改進(jìn)空間,將字符串匹配放在顯卡上進(jìn)行還可以進(jìn)一步提高字符讀取速度,提高字符匹配效率。

    參考文獻(xiàn)參考文獻(xiàn):

    \[1\]谷岳,谷建華.基于GPU加速的并行字符串匹配算法[J].微電子學(xué)與計(jì)算機(jī),2013(9):3033.

    [2]潘冠華,張興忠.Sunday算法效率分析[J].計(jì)算機(jī)應(yīng)用,2012(11):30823084,3088.

    [3]陳國良,林潔,顧乃杰. 分布式存儲(chǔ)的并行串匹配算法的設(shè)計(jì)與分析[J].軟件學(xué)報(bào),2000(6): 771778.

    [4]唐定車,劉任任,譚建龍.基于統(tǒng)一計(jì)算設(shè)備架構(gòu)的并行串匹配算法[J].計(jì)算機(jī)應(yīng)用,2009(1): 399401.

    [5][美]科克,胡文美.大規(guī)模并行處理器編程實(shí)戰(zhàn)[M].北京:清華大學(xué)出版社,2010:3177.

    責(zé)任編輯(責(zé)任編輯:杜能鋼)

    猜你喜歡
    并行計(jì)算
    基于Hadoop的民航日志分析系統(tǒng)及應(yīng)用
    基于自適應(yīng)線程束的GPU并行粒子群優(yōu)化算法
    云計(jì)算中MapReduce分布式并行處理框架的研究與搭建
    矩陣向量相乘的并行算法分析
    并行硬件簡介
    不可壓NS方程的高效并行直接求解
    基于GPU的超聲場仿真成像平臺(tái)
    基于Matlab的遙感圖像IHS小波融合算法的并行化設(shè)計(jì)
    科技視界(2016年11期)2016-05-23 08:13:35
    Spark計(jì)算引擎的數(shù)據(jù)對(duì)象緩存優(yōu)化研究
    大數(shù)據(jù)背景的IT平臺(tái)架構(gòu)探索
    科技視界(2015年30期)2015-10-22 11:44:33
    一区二区三区四区激情视频 | 欧美日韩中文字幕国产精品一区二区三区| 一区二区三区免费毛片| 人妻久久中文字幕网| 人妻丰满熟妇av一区二区三区| 好看av亚洲va欧美ⅴa在| 99久久久亚洲精品蜜臀av| avwww免费| 搡老妇女老女人老熟妇| 亚洲成a人片在线一区二区| 99久久精品一区二区三区| 夜夜看夜夜爽夜夜摸| 久久久成人免费电影| 欧美性猛交╳xxx乱大交人| 99在线视频只有这里精品首页| 国产综合懂色| 欧美区成人在线视频| 午夜福利欧美成人| 久久亚洲真实| 高清在线国产一区| 国产精品1区2区在线观看.| 亚洲av成人不卡在线观看播放网| 亚洲内射少妇av| 制服丝袜大香蕉在线| 国产日本99.免费观看| 啦啦啦韩国在线观看视频| 成年女人看的毛片在线观看| 欧美黑人欧美精品刺激| 麻豆成人午夜福利视频| 精品国内亚洲2022精品成人| av在线蜜桃| 丰满人妻一区二区三区视频av| 亚洲精华国产精华精| 精品日产1卡2卡| 欧美日韩国产亚洲二区| 精品久久久久久久久亚洲 | 日本黄色片子视频| 亚洲国产日韩欧美精品在线观看| 精品人妻视频免费看| 噜噜噜噜噜久久久久久91| 久久午夜亚洲精品久久| 尤物成人国产欧美一区二区三区| 亚洲成人免费电影在线观看| 亚洲av成人av| 欧美乱妇无乱码| 亚洲天堂国产精品一区在线| 不卡一级毛片| 亚洲av成人av| 在线看三级毛片| 中文字幕av在线有码专区| 欧美一区二区精品小视频在线| 精品午夜福利在线看| a在线观看视频网站| 精品久久久久久久久久久久久| 黄色日韩在线| 免费av毛片视频| 国产伦人伦偷精品视频| 18禁裸乳无遮挡免费网站照片| 日日干狠狠操夜夜爽| 国产精品不卡视频一区二区 | 大型黄色视频在线免费观看| 一区二区三区激情视频| 中文字幕人成人乱码亚洲影| 国产91精品成人一区二区三区| 国产精品,欧美在线| 午夜福利欧美成人| 2021天堂中文幕一二区在线观| 神马国产精品三级电影在线观看| 欧美三级亚洲精品| 婷婷六月久久综合丁香| 亚洲国产精品sss在线观看| 亚洲av二区三区四区| 免费在线观看日本一区| 中国美女看黄片| 长腿黑丝高跟| av天堂在线播放| 国产成人福利小说| 国产男靠女视频免费网站| 淫妇啪啪啪对白视频| 中文字幕久久专区| 国产精品美女特级片免费视频播放器| 欧美激情在线99| 综合色av麻豆| av在线天堂中文字幕| 露出奶头的视频| 日本 av在线| 亚洲精品日韩av片在线观看| 国产乱人视频| 日韩大尺度精品在线看网址| 国产探花在线观看一区二区| 搞女人的毛片| 日韩欧美国产在线观看| 级片在线观看| 淫妇啪啪啪对白视频| 国产熟女xx| av天堂中文字幕网| 大型黄色视频在线免费观看| 香蕉av资源在线| 日本a在线网址| 男女做爰动态图高潮gif福利片| 午夜免费成人在线视频| 大型黄色视频在线免费观看| 亚洲av中文字字幕乱码综合| 蜜桃久久精品国产亚洲av| 免费搜索国产男女视频| 国产国拍精品亚洲av在线观看| a级毛片免费高清观看在线播放| 88av欧美| 美女高潮喷水抽搐中文字幕| 久久精品影院6| 亚洲 国产 在线| 亚洲在线自拍视频| 久久久久精品国产欧美久久久| 色视频www国产| 国产在线精品亚洲第一网站| 午夜视频国产福利| 日韩欧美国产在线观看| 亚洲av成人精品一区久久| 美女被艹到高潮喷水动态| 国产亚洲精品av在线| 人妻制服诱惑在线中文字幕| 伊人久久精品亚洲午夜| 国产精品亚洲美女久久久| 99久久久亚洲精品蜜臀av| 一区二区三区高清视频在线| 亚洲乱码一区二区免费版| 亚洲美女视频黄频| 国产欧美日韩精品亚洲av| 国产精品爽爽va在线观看网站| 97热精品久久久久久| 国产精品永久免费网站| 色哟哟哟哟哟哟| 90打野战视频偷拍视频| 尤物成人国产欧美一区二区三区| 日本成人三级电影网站| 午夜福利在线在线| 最近中文字幕高清免费大全6 | 尤物成人国产欧美一区二区三区| 少妇熟女aⅴ在线视频| 亚洲欧美日韩无卡精品| 一个人免费在线观看电影| 国产高清有码在线观看视频| 亚洲av不卡在线观看| 亚洲va日本ⅴa欧美va伊人久久| 亚洲精品一区av在线观看| 日本 av在线| 亚洲成人中文字幕在线播放| 长腿黑丝高跟| 啪啪无遮挡十八禁网站| 亚洲欧美清纯卡通| 欧美成人一区二区免费高清观看| 简卡轻食公司| 91麻豆av在线| 级片在线观看| 成人高潮视频无遮挡免费网站| 一区二区三区激情视频| 欧美在线黄色| 成人特级av手机在线观看| 成人鲁丝片一二三区免费| 精品久久久久久久久久久久久| 欧美国产日韩亚洲一区| 简卡轻食公司| 精品久久久久久久久久免费视频| aaaaa片日本免费| 脱女人内裤的视频| h日本视频在线播放| 国产伦精品一区二区三区视频9| 我的女老师完整版在线观看| 久久精品影院6| 久久午夜福利片| 蜜桃久久精品国产亚洲av| 欧美激情久久久久久爽电影| 成人三级黄色视频| 天堂√8在线中文| 精品熟女少妇八av免费久了| 人妻丰满熟妇av一区二区三区| 在线观看66精品国产| 3wmmmm亚洲av在线观看| 99国产精品一区二区蜜桃av| 精品日产1卡2卡| 中文在线观看免费www的网站| 亚洲无线观看免费| 悠悠久久av| 偷拍熟女少妇极品色| aaaaa片日本免费| 好看av亚洲va欧美ⅴa在| 悠悠久久av| 久久久久久大精品| 久久精品国产99精品国产亚洲性色| 99久久九九国产精品国产免费| av欧美777| 色播亚洲综合网| 中出人妻视频一区二区| 99久久九九国产精品国产免费| 亚洲自拍偷在线| 国产精品精品国产色婷婷| 老司机福利观看| 又黄又爽又免费观看的视频| eeuss影院久久| 欧美激情在线99| 久久精品国产亚洲av天美| 欧美区成人在线视频| 亚洲片人在线观看| 精品久久久久久久末码| 久久久久久久亚洲中文字幕 | 在线观看一区二区三区| 亚洲自偷自拍三级| 国产精华一区二区三区| 精品久久久久久成人av| 熟女电影av网| 久久精品影院6| 可以在线观看的亚洲视频| 国产 一区 欧美 日韩| 男女那种视频在线观看| 色综合婷婷激情| 国产毛片a区久久久久| 国产乱人视频| 他把我摸到了高潮在线观看| 一级毛片久久久久久久久女| 久久草成人影院| 欧美+日韩+精品| 久久热精品热| 香蕉av资源在线| 国模一区二区三区四区视频| 很黄的视频免费| 波多野结衣巨乳人妻| 久久香蕉精品热| 美女大奶头视频| 国产欧美日韩精品亚洲av| 在线观看美女被高潮喷水网站 | 成人国产综合亚洲| 国产野战对白在线观看| av在线天堂中文字幕| 国内精品久久久久久久电影| 男女那种视频在线观看| 中文亚洲av片在线观看爽| 久久欧美精品欧美久久欧美| 俄罗斯特黄特色一大片| 99riav亚洲国产免费| www.熟女人妻精品国产| 伦理电影大哥的女人| 亚洲精品成人久久久久久| 男女之事视频高清在线观看| 女人被狂操c到高潮| 免费人成在线观看视频色| 1000部很黄的大片| 97人妻精品一区二区三区麻豆| 亚洲最大成人av| 午夜精品在线福利| 欧美极品一区二区三区四区| 99久久99久久久精品蜜桃| 好男人电影高清在线观看| 亚洲国产欧洲综合997久久,| 18禁裸乳无遮挡免费网站照片| 精品久久久久久久久久久久久| 99久久九九国产精品国产免费| 日韩中字成人| 综合色av麻豆| 午夜激情福利司机影院| 日日摸夜夜添夜夜添小说| 日韩精品青青久久久久久| 免费看美女性在线毛片视频| 特大巨黑吊av在线直播| 国产精品永久免费网站| 少妇高潮的动态图| 国语自产精品视频在线第100页| 精品99又大又爽又粗少妇毛片 | 亚洲中文日韩欧美视频| 成年女人看的毛片在线观看| 九色成人免费人妻av| 免费在线观看成人毛片| 99国产精品一区二区三区| 日韩中字成人| 日韩欧美免费精品| 特大巨黑吊av在线直播| 成人国产综合亚洲| 久久精品91蜜桃| 波多野结衣高清作品| 午夜精品在线福利| 色视频www国产| 国产精品久久电影中文字幕| 免费黄网站久久成人精品 | a级毛片a级免费在线| 无人区码免费观看不卡| 男女那种视频在线观看| 亚洲成人久久性| 亚洲av成人av| 国产淫片久久久久久久久 | 精品人妻偷拍中文字幕| 亚洲无线在线观看| 久99久视频精品免费| 亚洲在线观看片| 身体一侧抽搐| 有码 亚洲区| 51国产日韩欧美| 日韩中文字幕欧美一区二区| 久久天躁狠狠躁夜夜2o2o| 久久精品国产亚洲av涩爱 | 欧美精品啪啪一区二区三区| 国产一区二区三区在线臀色熟女| 亚洲中文日韩欧美视频| 欧美日韩中文字幕国产精品一区二区三区| 国产欧美日韩精品一区二区| 亚洲国产欧洲综合997久久,| 亚洲av成人精品一区久久| 婷婷六月久久综合丁香| 亚洲国产精品久久男人天堂| 精品国产三级普通话版| 国产成人啪精品午夜网站| 日本与韩国留学比较| 别揉我奶头~嗯~啊~动态视频| 亚洲中文字幕日韩| 国产精华一区二区三区| 欧美三级亚洲精品| 久久九九热精品免费| 一级黄色大片毛片| 日韩欧美精品免费久久 | 好男人在线观看高清免费视频| 在线a可以看的网站| 亚洲aⅴ乱码一区二区在线播放| 免费av观看视频| 国产精品三级大全| 99久久精品一区二区三区| 亚州av有码| 精品人妻一区二区三区麻豆 | 黄色日韩在线| 久久午夜福利片| 婷婷亚洲欧美| 亚洲国产精品成人综合色| 99国产精品一区二区三区| 欧美性感艳星| 搞女人的毛片| 两个人视频免费观看高清| 亚洲一区二区三区不卡视频| 亚洲av电影在线进入| 国产探花在线观看一区二区| 精品久久久久久久久av| 中文字幕久久专区| 亚洲精品粉嫩美女一区| 窝窝影院91人妻| 亚洲精品色激情综合| 精品久久久久久久久久久久久| 日本 av在线| 成人亚洲精品av一区二区| 一级a爱片免费观看的视频| 欧美丝袜亚洲另类 | 国产成人福利小说| 真人做人爱边吃奶动态| 国产亚洲欧美在线一区二区| 可以在线观看毛片的网站| 长腿黑丝高跟| 中文字幕久久专区| 亚洲国产欧美人成| 18+在线观看网站| 国产精品三级大全| 18+在线观看网站| 欧美性猛交黑人性爽| 国产探花在线观看一区二区| 亚洲国产欧美人成| 在线播放无遮挡| 国产一区二区三区在线臀色熟女| 91狼人影院| 淫秽高清视频在线观看| 国产精品人妻久久久久久| 九九热线精品视视频播放| 免费一级毛片在线播放高清视频| 床上黄色一级片| 午夜精品一区二区三区免费看| 日本精品一区二区三区蜜桃| 久久久精品大字幕| 国产成人福利小说| 国产亚洲精品综合一区在线观看| 超碰av人人做人人爽久久| 国产av麻豆久久久久久久| 亚洲自偷自拍三级| 国产伦精品一区二区三区四那| 精品久久久久久,| 亚洲av免费高清在线观看| 波多野结衣高清作品| 最近中文字幕高清免费大全6 | 久久精品综合一区二区三区| 亚洲第一欧美日韩一区二区三区| 亚洲第一区二区三区不卡| 日本免费a在线| 亚洲在线观看片| 少妇被粗大猛烈的视频| 精品熟女少妇八av免费久了| 亚洲经典国产精华液单 | 国产亚洲精品综合一区在线观看| 久久久久久久久大av| 久久久国产成人精品二区| 日韩欧美 国产精品| 国产精品久久久久久人妻精品电影| 免费一级毛片在线播放高清视频| 国产精品av视频在线免费观看| 国产日本99.免费观看| 日韩欧美 国产精品| 国产成人aa在线观看| 91字幕亚洲| 18禁黄网站禁片午夜丰满| 欧美又色又爽又黄视频| 国产精品伦人一区二区| 久久精品夜夜夜夜夜久久蜜豆| 精品久久久久久成人av| 丰满人妻一区二区三区视频av| 精品久久久久久久久久免费视频| 亚洲国产欧美人成| 亚洲一区二区三区不卡视频| 日韩av在线大香蕉| 日韩中文字幕欧美一区二区| 久99久视频精品免费| 国产精品影院久久| 如何舔出高潮| 久久久久久久久大av| 国产在线精品亚洲第一网站| 国产亚洲欧美在线一区二区| 久久久久久久久久成人| 日韩av在线大香蕉| 亚洲 欧美 日韩 在线 免费| 国产美女午夜福利| 亚洲国产精品999在线| 亚洲人成网站在线播| 国产三级在线视频| 首页视频小说图片口味搜索| av国产免费在线观看| 欧美高清性xxxxhd video| 色综合亚洲欧美另类图片| 99热这里只有是精品50| 女生性感内裤真人,穿戴方法视频| 欧美高清成人免费视频www| 日本免费a在线| 亚洲色图av天堂| 最后的刺客免费高清国语| 亚洲一区二区三区色噜噜| 精品熟女少妇八av免费久了| 亚洲自拍偷在线| 精品99又大又爽又粗少妇毛片 | 久久久久九九精品影院| 国产精品综合久久久久久久免费| 欧美3d第一页| 草草在线视频免费看| 天堂影院成人在线观看| 久久精品影院6| 99久久99久久久精品蜜桃| 51午夜福利影视在线观看| av福利片在线观看| 别揉我奶头~嗯~啊~动态视频| 亚洲精品在线观看二区| 婷婷丁香在线五月| 欧美黄色片欧美黄色片| a级一级毛片免费在线观看| 免费看美女性在线毛片视频| 亚洲专区国产一区二区| 99在线视频只有这里精品首页| 神马国产精品三级电影在线观看| 亚洲av电影不卡..在线观看| 丰满人妻一区二区三区视频av| 宅男免费午夜| 国内久久婷婷六月综合欲色啪| 日韩欧美三级三区| 欧美高清成人免费视频www| 最近中文字幕高清免费大全6 | 嫩草影视91久久| 久久精品国产99精品国产亚洲性色| 久久精品夜夜夜夜夜久久蜜豆| 久久人妻av系列| 色综合站精品国产| 国产毛片a区久久久久| 亚洲欧美清纯卡通| 午夜福利在线在线| 日本三级黄在线观看| 亚洲18禁久久av| 小蜜桃在线观看免费完整版高清| 亚洲av熟女| 欧美三级亚洲精品| 99久久精品国产亚洲精品| 亚洲国产精品sss在线观看| 亚洲不卡免费看| 欧美黑人欧美精品刺激| 色5月婷婷丁香| 精品久久久久久久末码| 欧美一区二区精品小视频在线| 女人被狂操c到高潮| 日韩欧美一区二区三区在线观看| 国产伦精品一区二区三区四那| 搡老妇女老女人老熟妇| 动漫黄色视频在线观看| aaaaa片日本免费| 久久这里只有精品中国| 国产av麻豆久久久久久久| 精品免费久久久久久久清纯| 全区人妻精品视频| 99久久精品国产亚洲精品| 搡女人真爽免费视频火全软件 | 在现免费观看毛片| 午夜福利18| 99热这里只有精品一区| www.999成人在线观看| 国产午夜精品论理片| 中亚洲国语对白在线视频| 成人毛片a级毛片在线播放| 老司机午夜福利在线观看视频| 国产精品,欧美在线| 免费av观看视频| 天天躁日日操中文字幕| 亚洲专区中文字幕在线| 国产精品久久电影中文字幕| 国产一区二区在线av高清观看| 在线十欧美十亚洲十日本专区| 男插女下体视频免费在线播放| 又粗又爽又猛毛片免费看| 中文字幕免费在线视频6| 一二三四社区在线视频社区8| 亚洲,欧美,日韩| 亚洲欧美清纯卡通| 亚洲美女黄片视频| 天堂影院成人在线观看| 我要看日韩黄色一级片| 国产精品亚洲一级av第二区| aaaaa片日本免费| 日韩欧美一区二区三区在线观看| 久久久久久久久中文| 嫩草影院入口| 此物有八面人人有两片| 99久久成人亚洲精品观看| 丰满乱子伦码专区| 变态另类成人亚洲欧美熟女| bbb黄色大片| 色噜噜av男人的天堂激情| 啦啦啦韩国在线观看视频| 51午夜福利影视在线观看| 国产一级毛片七仙女欲春2| 国产单亲对白刺激| 欧美精品国产亚洲| 99久久99久久久精品蜜桃| 97热精品久久久久久| 国产精品影院久久| 国产大屁股一区二区在线视频| 国产精品自产拍在线观看55亚洲| 三级男女做爰猛烈吃奶摸视频| 中文字幕精品亚洲无线码一区| 最新中文字幕久久久久| 亚洲av中文字字幕乱码综合| 国产精品久久视频播放| 久久久久亚洲av毛片大全| 亚洲国产精品久久男人天堂| 90打野战视频偷拍视频| 波野结衣二区三区在线| 国内精品久久久久久久电影| 国产私拍福利视频在线观看| 国产成+人综合+亚洲专区| 99riav亚洲国产免费| 亚洲美女黄片视频| 亚洲欧美日韩高清在线视频| 亚洲av熟女| 欧美三级亚洲精品| 无人区码免费观看不卡| 亚洲国产精品999在线| 淫妇啪啪啪对白视频| 狠狠狠狠99中文字幕| 国产高潮美女av| 欧美高清性xxxxhd video| 露出奶头的视频| 夜夜看夜夜爽夜夜摸| 中出人妻视频一区二区| 床上黄色一级片| 黄色日韩在线| 桃色一区二区三区在线观看| 国产高清视频在线观看网站| 国产精品国产高清国产av| 国产成人av教育| 日韩欧美一区二区三区在线观看| 搡老熟女国产l中国老女人| 欧美成人一区二区免费高清观看| 999久久久精品免费观看国产| 精品熟女少妇八av免费久了| av天堂在线播放| 极品教师在线视频| 男女下面进入的视频免费午夜| 欧美国产日韩亚洲一区| 精品乱码久久久久久99久播| 亚洲三级黄色毛片| 噜噜噜噜噜久久久久久91| 99国产精品一区二区三区| 日本 欧美在线| 亚洲电影在线观看av| 热99re8久久精品国产| 亚洲精品日韩av片在线观看| 日本三级黄在线观看| 亚洲18禁久久av| 亚洲成av人片在线播放无| 欧美成人性av电影在线观看| 麻豆成人av在线观看| 在现免费观看毛片| 国产男靠女视频免费网站| 99热这里只有精品一区| 精品午夜福利在线看| av专区在线播放| 亚洲av一区综合| 亚洲人成网站在线播放欧美日韩| 能在线免费观看的黄片| 午夜福利18| 国产在视频线在精品| 变态另类丝袜制服| 内射极品少妇av片p| 嫁个100分男人电影在线观看| 好男人电影高清在线观看| 欧美成人免费av一区二区三区| 丰满人妻一区二区三区视频av| 看黄色毛片网站| 一区二区三区四区激情视频 | 757午夜福利合集在线观看| 中国美女看黄片| 午夜福利在线观看免费完整高清在 | 少妇人妻一区二区三区视频|